| /third_party/mesa3d/src/intel/compiler/ |
| D | brw_nir_rt_builder.h | 321 defs->hw_stack_size = nir_channel(b, data, 4); in brw_nir_rt_load_globals_addr()
322 defs->num_dss_rt_stacks = nir_iand_imm(b, nir_channel(b, data, 5), 0xffff); in brw_nir_rt_load_globals_addr()
324 nir_pack_64_2x32_split(b, nir_channel(b, data, 8), in brw_nir_rt_load_globals_addr()
325 nir_extract_i16(b, nir_channel(b, data, 9), in brw_nir_rt_load_globals_addr()
328 nir_unpack_32_2x16_split_y(b, nir_channel(b, data, 9)); in brw_nir_rt_load_globals_addr()
330 nir_pack_64_2x32_split(b, nir_channel(b, data, 10), in brw_nir_rt_load_globals_addr()
331 nir_extract_i16(b, nir_channel(b, data, 11), in brw_nir_rt_load_globals_addr()
334 nir_unpack_32_2x16_split_y(b, nir_channel(b, data, 11)); in brw_nir_rt_load_globals_addr()
335 defs->sw_stack_size = nir_channel(b, data, 12); in brw_nir_rt_load_globals_addr()
340 nir_pack_64_2x32_split(b, nir_channel(b, data, 0), in brw_nir_rt_load_globals_addr()
[all …]
|
| D | brw_nir_lower_storage_image.c | 74 in_bounds = nir_iand(b, in_bounds, nir_channel(b, cmp, i)); in image_coord_is_in_bounds()
98 coord = nir_vec3(b, nir_channel(b, coord, 0), in image_address()
100 nir_channel(b, coord, 1)); in image_address()
148 nir_ssa_def *z = nir_channel(b, coord, 2); in image_address()
150 nir_channel(b, tiling, 2)); in image_address()
151 nir_ssa_def *z_y = nir_ushr(b, z, nir_channel(b, tiling, 2)); in image_address()
189 idx_x = nir_ishl(b, nir_channel(b, major, 0), nir_channel(b, tiling, 1)); in image_address()
190 idx_x = nir_iadd(b, idx_x, nir_channel(b, minor, 1)); in image_address()
191 idx_x = nir_ishl(b, idx_x, nir_channel(b, tiling, 0)); in image_address()
192 idx_x = nir_iadd(b, idx_x, nir_channel(b, minor, 0)); in image_address()
[all …]
|
| /third_party/mesa3d/src/intel/blorp/ |
| D | blorp_nir_builder.h | 50 coord = nir_vec3(b, nir_channel(b, xy_pos, 0), in blorp_nir_txf_ms_mcs()
51 nir_channel(b, xy_pos, 1), in blorp_nir_txf_ms_mcs()
81 return nir_ieq_imm(b, nir_iand(b, nir_channel(b, mcs, 0), in blorp_nir_mcs_is_clear_color()
86 return nir_ieq_imm(b, nir_channel(b, mcs, 0), 0xff); in blorp_nir_mcs_is_clear_color()
89 return nir_ieq_imm(b, nir_channel(b, mcs, 0), ~0); in blorp_nir_mcs_is_clear_color()
93 return nir_iand(b, nir_ieq_imm(b, nir_channel(b, mcs, 0), ~0), in blorp_nir_mcs_is_clear_color()
94 nir_ieq_imm(b, nir_channel(b, mcs, 1), ~0)); in blorp_nir_mcs_is_clear_color()
106 nir_ssa_def *x0 = nir_channel(b, bounds_rect, 0); in blorp_check_in_bounds()
107 nir_ssa_def *x1 = nir_channel(b, bounds_rect, 1); in blorp_check_in_bounds()
108 nir_ssa_def *y0 = nir_channel(b, bounds_rect, 2); in blorp_check_in_bounds()
[all …]
|
| /third_party/mesa3d/src/microsoft/vulkan/ |
| D | dzn_nir.c | 81 return nir_channel(b, desc, 0); in dzn_nir_create_bo_desc()
146 nir_ssa_def *draw_stride = nir_channel(&b, params, 0); in dzn_nir_indirect_draw_shader()
152 nir_channel(&b, nir_load_global_invocation_id(&b, 32), 0); in dzn_nir_indirect_draw_shader()
186 nir_ssa_def *first_vertex = nir_channel(&b, draw_info1, indexed ? 3 : 2); in dzn_nir_indirect_draw_shader()
188 indexed ? draw_info2 : nir_channel(&b, draw_info1, 3); in dzn_nir_indirect_draw_shader()
199 nir_usub_sat(&b, nir_channel(&b, draw_info1, 0), nir_imm_int(&b, 2)); in dzn_nir_indirect_draw_shader()
201 exec_vals[4] = nir_channel(&b, draw_info1, 1); in dzn_nir_indirect_draw_shader()
210 nir_ssa_def *triangle_fan_index_buf_stride = nir_channel(&b, params, 1); in dzn_nir_indirect_draw_shader()
212 nir_iadd(&b, nir_channel(&b, params, 2), in dzn_nir_indirect_draw_shader()
218 nir_ult(&b, triangle_fan_index_buf_addr_lo, nir_channel(&b, params, 2)); in dzn_nir_indirect_draw_shader()
[all …]
|
| /third_party/mesa3d/src/compiler/nir/ |
| D | nir_lower_packing.c | 40 return nir_pack_64_2x32_split(b, nir_channel(b, src, 0), in lower_pack_64_from_32()
41 nir_channel(b, src, 1)); in lower_pack_64_from_32()
54 return nir_pack_32_2x16_split(b, nir_channel(b, src, 0), in lower_pack_32_from_16()
55 nir_channel(b, src, 1)); in lower_pack_32_from_16()
68 nir_ssa_def *xy = nir_pack_32_2x16_split(b, nir_channel(b, src, 0), in lower_pack_64_from_16()
69 nir_channel(b, src, 1)); in lower_pack_64_from_16()
71 nir_ssa_def *zw = nir_pack_32_2x16_split(b, nir_channel(b, src, 2), in lower_pack_64_from_16()
72 nir_channel(b, src, 3)); in lower_pack_64_from_16()
92 return nir_pack_32_4x8_split(b, nir_channel(b, src, 0), in lower_pack_32_from_8()
93 nir_channel(b, src, 1), in lower_pack_32_from_8()
[all …]
|
| D | nir_lower_wpos_ytransform.c | 104 nir_channel(b, wpostrans, invert ? 2 : 0), in emit_wpos_adjustment()
126 wpos_temp_y = nir_fadd(b, nir_fmul(b, nir_channel(b, wpos_temp, 1), in emit_wpos_adjustment()
127 nir_channel(b, wpostrans, 0)), in emit_wpos_adjustment()
128 nir_channel(b, wpostrans, 1)); in emit_wpos_adjustment()
131 wpos_temp_y = nir_fadd(b, nir_fmul(b, nir_channel(b, wpos_temp, 1), in emit_wpos_adjustment()
132 nir_channel(b, wpostrans, 2)), in emit_wpos_adjustment()
133 nir_channel(b, wpostrans, 3)); in emit_wpos_adjustment()
137 nir_channel(b, wpos_temp, 0), in emit_wpos_adjustment()
139 nir_channel(b, wpos_temp, 2), in emit_wpos_adjustment()
140 nir_channel(b, wpos_temp, 3)); in emit_wpos_adjustment()
[all …]
|
| D | nir_lower_tex.c | 132 nir_channel(b, projected, 0), in project_src()
133 nir_channel(b, projected, 1), in project_src()
134 nir_channel(b, projected, 2), in project_src()
135 nir_channel(b, unprojected, 3)); in project_src()
139 nir_channel(b, projected, 0), in project_src()
140 nir_channel(b, projected, 1), in project_src()
141 nir_channel(b, unprojected, 2)); in project_src()
145 nir_channel(b, projected, 0), in project_src()
146 nir_channel(b, unprojected, 1)); in project_src()
200 offset_coord = nir_vec2(b, nir_channel(b, offset_coord, 0), in lower_offset()
[all …]
|
| D | nir_lower_point_size_mov.c | 68 …load = nir_fclamp(&b, nir_channel(&b, load, 0), nir_channel(&b, load, 1), nir_channel(&b, load, 2)… in lower_impl()
81 …load = nir_fclamp(&b, nir_channel(&b, load, 0), nir_channel(&b, load, 1), nir_channel(&b, load, 2)… in lower_impl()
92 …load = nir_fclamp(&b, nir_channel(&b, load, 0), nir_channel(&b, load, 1), nir_channel(&b, load, 2)… in lower_impl()
|
| D | nir_lower_blend.c | 85 nir_ssa_def *Asrc = nir_channel(b, src, 3); in nir_alpha_saturate()
86 nir_ssa_def *Adst = nir_channel(b, dst, 3); in nir_alpha_saturate()
106 return nir_channel(b, src, chan); in nir_blend_factor_value()
108 return nir_channel(b, src1, chan); in nir_blend_factor_value()
110 return nir_channel(b, dst, chan); in nir_blend_factor_value()
112 return nir_channel(b, src, 3); in nir_blend_factor_value()
114 return nir_channel(b, src1, 3); in nir_blend_factor_value()
116 return nir_channel(b, dst, 3); in nir_blend_factor_value()
118 return nir_channel(b, bconst, chan); in nir_blend_factor_value()
120 return nir_channel(b, bconst, 3); in nir_blend_factor_value()
[all …]
|
| D | nir_lower_alu_width.c | 227 return nir_pack_half_2x16_split(b, nir_channel(b, src_vec2, 0), in lower_alu_instr_width()
228 nir_channel(b, src_vec2, 1)); in lower_alu_instr_width()
265 return nir_ior(b, nir_ishl(b, nir_channel(b, word, 1), in lower_alu_instr_width()
267 nir_channel(b, word, 0)); in lower_alu_instr_width()
276 return nir_ior(b, nir_ior(b, nir_ishl(b, nir_channel(b, byte, 3), in lower_alu_instr_width()
278 nir_ishl(b, nir_channel(b, byte, 2), in lower_alu_instr_width()
280 nir_ior(b, nir_ishl(b, nir_channel(b, byte, 1), in lower_alu_instr_width()
282 nir_channel(b, byte, 0))); in lower_alu_instr_width()
291 sum[i] = nir_fmul(b, nir_channel(b, src0_vec, i), in lower_alu_instr_width()
292 nir_channel(b, src1_vec, i)); in lower_alu_instr_width()
[all …]
|
| D | nir_normalize_cubemap_coords.c | 60 nir_ssa_def *norm = nir_fmax(b, nir_channel(b, abs, 0), in normalize_cubemap_coords_block()
61 nir_fmax(b, nir_channel(b, abs, 1), in normalize_cubemap_coords_block()
62 nir_channel(b, abs, 2))); in normalize_cubemap_coords_block()
71 nir_channel(b, normalized, 0), in normalize_cubemap_coords_block()
72 nir_channel(b, normalized, 1), in normalize_cubemap_coords_block()
73 nir_channel(b, normalized, 2), in normalize_cubemap_coords_block()
74 nir_channel(b, orig_coord, 3)); in normalize_cubemap_coords_block()
|
| D | nir_lower_system_values.c | 283 nir_ssa_def *size_x = nir_channel(b, size, 0); in lower_id_to_index_no_umod()
284 nir_ssa_def *size_y = nir_channel(b, size, 1); in lower_id_to_index_no_umod()
317 nir_ssa_def *size_x = nir_channel(b, size, 0); in lower_id_to_index()
318 nir_ssa_def *size_y = nir_channel(b, size, 1); in lower_id_to_index()
365 nir_ssa_def *x = nir_channel(b, ids, 0); in lower_compute_system_value_instr()
366 nir_ssa_def *y = nir_channel(b, ids, 1); in lower_compute_system_value_instr()
367 nir_ssa_def *z = nir_channel(b, ids, 2); in lower_compute_system_value_instr()
372 size_x_imm = nir_channel(b, nir_load_workgroup_size(b), 0); in lower_compute_system_value_instr()
467 nir_ssa_def *size_x = nir_channel(b, local_size, 0); in lower_compute_system_value_instr()
468 nir_ssa_def *size_y = nir_channel(b, local_size, 1); in lower_compute_system_value_instr()
[all …]
|
| D | nir_format_convert.h | 82 comps[i] = nir_ishr(b, nir_ishl(b, nir_channel(b, src, i), shift), shift); in nir_format_sign_extend_ivec()
108 nir_ssa_def *chan = nir_channel(b, packed, next_chan); in nir_format_unpack_int()
147 packed = nir_ior(b, packed, nir_shift_imm(b, nir_channel(b, color, i), in nir_format_pack_uint_unmasked()
163 packed = nir_ior(b, packed, nir_ishl(b, nir_channel(b, color, i), offset)); in nir_format_pack_uint_unmasked_ssa()
164 offset = nir_iadd(b, offset, nir_channel(b, bits, i)); in nir_format_pack_uint_unmasked_ssa()
197 nir_ssa_def *shifted = nir_ishl(b, nir_channel(b, src, i), in nir_format_bitcast_uvec_unmasked()
217 dst_chan[i] = nir_iand(b, nir_ushr_imm(b, nir_channel(b, src, src_idx), in nir_format_bitcast_uvec_unmasked()
297 f16comps[i] = nir_pack_half_2x16_split(b, nir_channel(b, f, i), zero); in nir_format_float_to_half()
389 nir_ssa_def *p1 = nir_pack_half_2x16_split(b, nir_channel(b, clamped, 0), in nir_format_pack_11f11f10f()
390 nir_channel(b, clamped, 1)); in nir_format_pack_11f11f10f()
[all …]
|
| D | nir_lower_clip_halfz.c | 45 nir_channel(b, pos, 0), in lower_pos_write()
46 nir_channel(b, pos, 1), in lower_pos_write()
49 nir_channel(b, pos, 2), in lower_pos_write()
50 nir_channel(b, pos, 3)), in lower_pos_write()
52 nir_channel(b, pos, 3)); in lower_pos_write()
|
| /third_party/mesa3d/src/amd/vulkan/ |
| D | radv_rt_common.c | 54 b, nir_flt(b, nir_channel(b, ssa_distances, chan_2), nir_channel(b, ssa_distances, chan_1))); in nir_sort_hit_pair()
61 new_distances[chan_2] = nir_channel(b, ssa_distances, chan_1); in nir_sort_hit_pair()
62 new_distances[chan_1] = nir_channel(b, ssa_distances, chan_2); in nir_sort_hit_pair()
63 new_indices[chan_2] = nir_channel(b, ssa_indices, chan_1); in nir_sort_hit_pair()
64 new_indices[chan_1] = nir_channel(b, ssa_indices, chan_2); in nir_sort_hit_pair()
122 nir_ssa_def *min_x = nir_channel(b, node_coords[0], 0); in intersect_ray_amd_software_box()
135 nir_fmax(b, nir_fmin(b, nir_channel(b, bound0, 0), nir_channel(b, bound1, 0)), in intersect_ray_amd_software_box()
136 nir_fmin(b, nir_channel(b, bound0, 1), nir_channel(b, bound1, 1))), in intersect_ray_amd_software_box()
137 nir_fmin(b, nir_channel(b, bound0, 2), nir_channel(b, bound1, 2))); in intersect_ray_amd_software_box()
143 nir_fmin(b, nir_fmax(b, nir_channel(b, bound0, 0), nir_channel(b, bound1, 0)), in intersect_ray_amd_software_box()
[all …]
|
| D | radv_nir_apply_pipeline_layout.c | 126 nir_ssa_def *binding_ptr = nir_channel(b, intrin->src[0].ssa, 1); in visit_vulkan_resource_reindex()
127 nir_ssa_def *stride = nir_channel(b, intrin->src[0].ssa, 2); in visit_vulkan_resource_reindex()
192 rsrc = nir_iadd(b, nir_channel(b, rsrc, 0), nir_channel(b, rsrc, 1)); in load_buffer_descriptor()
198 return nir_iadd(b, nir_channel(b, rsrc, 0), nir_channel(b, rsrc, 1)); in load_buffer_descriptor()
200 nir_ssa_def *desc_set = convert_pointer_to_64_bit(b, state, nir_channel(b, rsrc, 0)); in load_buffer_descriptor()
201 return nir_load_smem_amd(b, 4, desc_set, nir_channel(b, rsrc, 1), .align_mul = 16); in load_buffer_descriptor()
211 nir_ssa_def *ptr = nir_iadd(b, nir_channel(b, rsrc, 0), nir_channel(b, rsrc, 1)); in visit_get_ssbo_size()
219 nir_ssa_def *ptr = convert_pointer_to_64_bit(b, state, nir_channel(b, rsrc, 0)); in visit_get_ssbo_size()
220 nir_ssa_def *desc = nir_load_smem_amd(b, 4, ptr, nir_channel(b, rsrc, 1), .align_mul = 16); in visit_get_ssbo_size()
221 size = nir_channel(b, desc, 2); in visit_get_ssbo_size()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/d3d12/ |
| D | d3d12_lower_image_casts.c | 63 channels[i] = nir_channel(b, value, i); in convert_value()
121 return nir_vec4(b, nir_channel(b, vec3, 0), in convert_value()
122 nir_channel(b, vec3, 1), in convert_value()
123 nir_channel(b, vec3, 2), in convert_value()
130 nir_ssa_def *unpacked = nir_unpack_unorm_4x8(b, nir_channel(b, dest_packed, 0)); in convert_value()
136 nir_unpack_unorm_2x16(b, nir_channel(b, dest_packed, 0)), in convert_value()
138 nir_unpack_unorm_2x16(b, nir_channel(b, dest_packed, 1)) : in convert_value()
143 return nir_vec4(b, nir_channel(b, vec2s[0], 0), in convert_value()
144 nir_channel(b, vec2s[0], 1), in convert_value()
145 nir_channel(b, vec2s[1], 0), in convert_value()
[all …]
|
| D | d3d12_lower_point_sprite.c | 121 point_size = nir_channel(b, uniform, 2); in get_scaled_point_size()
124 point_size = nir_fmul(b, point_size, nir_channel(b, state->point_pos, 3)); in get_scaled_point_size()
125 *x = nir_fmul(b, point_size, nir_channel(b, uniform, 0)); in get_scaled_point_size()
126 *y = nir_fmul(b, point_size, nir_channel(b, uniform, 1)); in get_scaled_point_size()
180 nir_channel(b, point_dir, 0), in lower_emit_vertex()
181 nir_channel(b, state->point_pos, 0)), in lower_emit_vertex()
184 nir_channel(b, point_dir, 1), in lower_emit_vertex()
185 nir_channel(b, state->point_pos, 1)), in lower_emit_vertex()
186 nir_channel(b, state->point_pos, 2), in lower_emit_vertex()
187 nir_channel(b, state->point_pos, 3)); in lower_emit_vertex()
|
| /third_party/mesa3d/src/gallium/auxiliary/nir/ |
| D | nir_draw_helpers.c | 92 nir_ssa_def *condition = nir_f2b32(b, nir_channel(b, &tex->dest.ssa, 3)); in nir_lower_pstipple_block()
177 nir_ssa_def *tmp = nir_fsat(b, nir_fadd(b, nir_channel(b, lw, 1), in nir_lower_aaline_block()
178 nir_fneg(b, nir_fabs(b, nir_channel(b, lw, 0))))); in nir_lower_aaline_block()
179 nir_ssa_def *tmp1 = nir_fsat(b, nir_fadd(b, nir_channel(b, lw, 3), in nir_lower_aaline_block()
180 nir_fneg(b, nir_fabs(b, nir_channel(b, lw, 2))))); in nir_lower_aaline_block()
183 tmp = nir_fmul(b, nir_channel(b, out_input, 3), tmp); in nir_lower_aaline_block()
185 nir_ssa_def *out = nir_vec4(b, nir_channel(b, out_input, 0), in nir_lower_aaline_block()
186 nir_channel(b, out_input, 1), in nir_lower_aaline_block()
187 nir_channel(b, out_input, 2), in nir_lower_aaline_block()
272 nir_ssa_def *tmp = nir_fmul(b, nir_channel(b, out_input, 3), sel); in nir_lower_aapoint_block()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/lima/ir/ |
| D | lima_nir_lower_txp.c | 136 nir_channel(b, coords_ssa, 0), in lima_nir_lower_txp_instr()
137 nir_channel(b, coords_ssa, 0), in lima_nir_lower_txp_instr()
138 nir_channel(b, proj_ssa, 0)); in lima_nir_lower_txp_instr()
143 nir_channel(b, coords_ssa, 0), in lima_nir_lower_txp_instr()
144 nir_channel(b, coords_ssa, 1), in lima_nir_lower_txp_instr()
145 nir_channel(b, proj_ssa, 0)); in lima_nir_lower_txp_instr()
150 nir_channel(b, coords_ssa, 0), in lima_nir_lower_txp_instr()
151 nir_channel(b, coords_ssa, 1), in lima_nir_lower_txp_instr()
152 nir_channel(b, coords_ssa, 2), in lima_nir_lower_txp_instr()
153 nir_channel(b, proj_ssa, 0)); in lima_nir_lower_txp_instr()
|
| /third_party/mesa3d/src/panfrost/util/ |
| D | pan_lower_framebuffer.c | 116 replicated[i] = nir_channel(b, v, i % num_components); in pan_replicate()
150 nir_unpack_32_2x16(b, nir_channel(b, pack, i >> 1)); in pan_unpack_pure_16()
152 unpacked[i + 0] = nir_channel(b, halves, 0); in pan_unpack_pure_16()
153 unpacked[i + 1] = nir_channel(b, halves, 1); in pan_unpack_pure_16()
204 nir_ssa_def *unpacked = nir_unpack_32_4x8(b, nir_channel(b, pack, 0)); in pan_unpack_pure_8()
275 nir_ishl(b, nir_channel(b, bottom2, 0), nir_imm_int(b, 24 + 0)), in pan_pack_unorm_1010102()
276 nir_ishl(b, nir_channel(b, bottom2, 1), nir_imm_int(b, 24 + 2))), in pan_pack_unorm_1010102()
278 nir_ishl(b, nir_channel(b, bottom2, 2), nir_imm_int(b, 24 + 4)), in pan_pack_unorm_1010102()
279 nir_ishl(b, nir_channel(b, bottom2, 3), nir_imm_int(b, 24 + 6)))); in pan_pack_unorm_1010102()
302 nir_ior(b, nir_channel(b, v, 0), nir_channel(b, v, 1)), in pan_pack_int_1010102()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/r600/sfn/ |
| D | sfn_nir_lower_tex.cpp | 45 corr = nir_vec3(b, nir_channel(b, corr2, 0), nir_channel(b, corr2, 1), in lower_coord_shift_normalized()
46 nir_channel( in lower_coord_shift_normalized()
67 corr = nir_vec3(b, nir_channel(b, corr2, 0), nir_channel(b, corr2, 1), in lower_coord_shift_unnormalized()
68 nir_channel(b, tex->src[coord_index].src.ssa, 2)); in lower_coord_shift_unnormalized()
263 nir_vec2(b, nir_channel(b, cubed, 1), nir_channel(b, cubed, 0)), in r600_nir_lower_cube_to_2darray_impl()
264 nir_frcp(b, nir_fabs(b, nir_channel(b, cubed, 2))), in r600_nir_lower_cube_to_2darray_impl()
267 nir_ssa_def *z = nir_channel(b, cubed, 3); in r600_nir_lower_cube_to_2darray_impl()
269 auto slice = nir_fround_even(b, nir_channel(b, tex->src[coord_idx].src.ssa, 3)); in r600_nir_lower_cube_to_2darray_impl()
285 auto new_coord = nir_vec3(b, nir_channel(b, xy, 0), nir_channel(b, xy, 1), z); in r600_nir_lower_cube_to_2darray_impl()
|
| D | sfn_nir_lower_tess_io.cpp | 112 return r600_umad_24(b, nir_channel(b, param_base, 0), in r600_tcs_base_address()
114 nir_channel(b, param_base, 3)); in r600_tcs_base_address()
122 nir_channel(b, base, 0), in emil_lsd_in_addr()
127 addr = r600_umad_24(b, nir_channel(b, base, 1), in emil_lsd_in_addr()
144 nir_ssa_def *addr1 = r600_umad_24(b, nir_channel(b, base, 0), in emil_lsd_out_addr()
146 nir_channel(b, base, 2)); in emil_lsd_out_addr()
147 nir_ssa_def *addr2 = r600_umad_24(b, nir_channel(b, base, 1), in emil_lsd_out_addr()
258 remix[i] = nir_channel(b, new_load, chan++); in replace_load_instr()
354 vertices_in = nir_channel(b, load_in_param_base, 2); in r600_lower_tess_io_impl()
357 vertices_in = nir_channel(b, base, 2); in r600_lower_tess_io_impl()
[all …]
|
| /third_party/mesa3d/src/panfrost/vulkan/ |
| D | panvk_vX_nir_lower_descriptors.c | 176 return nir_vec2(b, nir_channel(b, orig, 0), in build_res_reindex()
177 nir_iadd(b, nir_channel(b, orig, 1), delta)); in build_res_reindex()
181 return nir_vec4(b, nir_channel(b, orig, 0), in build_res_reindex()
182 nir_channel(b, orig, 1), in build_res_reindex()
183 nir_channel(b, orig, 2), in build_res_reindex()
184 nir_iadd(b, nir_channel(b, orig, 3), delta)); in build_res_reindex()
206 nir_ssa_def *packed = nir_channel(b, res_index, 0); in build_buffer_addr_for_res_index()
207 nir_ssa_def *array_index = nir_channel(b, res_index, 1); in build_buffer_addr_for_res_index()
220 nir_ssa_def *packed = nir_channel(b, res_index, 0); in build_buffer_addr_for_res_index()
221 nir_ssa_def *desc_ubo_offset = nir_channel(b, res_index, 1); in build_buffer_addr_for_res_index()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/radeonsi/ |
| D | si_shaderlib_nir.c | 155 nir_ssa_def *src_dcc_offset = nir_channel(&b, user_sgprs, 0); in si_create_dcc_retile_cs()
158 unpack_2x16(&b, nir_channel(&b, user_sgprs, 1), &src_dcc_pitch, &src_dcc_height); in si_create_dcc_retile_cs()
159 unpack_2x16(&b, nir_channel(&b, user_sgprs, 2), &dst_dcc_pitch, &dst_dcc_height); in si_create_dcc_retile_cs()
172 nir_channel(&b, coord, 0), nir_channel(&b, coord, 1), /* x, y */ in si_create_dcc_retile_cs()
180 nir_channel(&b, coord, 0), nir_channel(&b, coord, 1), /* x, y */ in si_create_dcc_retile_cs()
202 unpack_2x16(&b, nir_channel(&b, user_sgprs, 0), &dcc_pitch, &dcc_height); in gfx9_create_clear_dcc_msaa_cs()
203 unpack_2x16(&b, nir_channel(&b, user_sgprs, 1), &clear_value, &pipe_xor); in gfx9_create_clear_dcc_msaa_cs()
220 nir_channel(&b, coord, 0), nir_channel(&b, coord, 1), /* x, y */ in gfx9_create_clear_dcc_msaa_cs()
221 … tex->buffer.b.b.array_size > 1 ? nir_channel(&b, coord, 2) : zero, /* z */ in gfx9_create_clear_dcc_msaa_cs()
260 data = nir_iand(&b, data, nir_channel(&b, user_sgprs, 1)); in si_create_clear_buffer_rmw_cs()
[all …]
|