| /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/intel/compiler/ |
| D | brw_nir_rt_builder.h | 220 defs->hw_stack_size = nir_channel(b, data, 4); in brw_nir_rt_load_globals()
221 defs->num_dss_rt_stacks = nir_iand_imm(b, nir_channel(b, data, 5), 0xffff); in brw_nir_rt_load_globals()
223 nir_pack_64_2x32_split(b, nir_channel(b, data, 8), in brw_nir_rt_load_globals()
224 nir_extract_i16(b, nir_channel(b, data, 9), in brw_nir_rt_load_globals()
227 nir_unpack_32_2x16_split_y(b, nir_channel(b, data, 9)); in brw_nir_rt_load_globals()
229 nir_pack_64_2x32_split(b, nir_channel(b, data, 10), in brw_nir_rt_load_globals()
230 nir_extract_i16(b, nir_channel(b, data, 11), in brw_nir_rt_load_globals()
233 nir_unpack_32_2x16_split_y(b, nir_channel(b, data, 11)); in brw_nir_rt_load_globals()
234 defs->sw_stack_size = nir_channel(b, data, 12); in brw_nir_rt_load_globals()
240 nir_pack_64_2x32_split(b, nir_channel(b, data, 0), in brw_nir_rt_load_globals()
[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/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_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_tex.c | 106 nir_channel(b, projected, 0), in project_src()
107 nir_channel(b, projected, 1), in project_src()
108 nir_channel(b, projected, 2), in project_src()
109 nir_channel(b, unprojected, 3)); in project_src()
113 nir_channel(b, projected, 0), in project_src()
114 nir_channel(b, projected, 1), in project_src()
115 nir_channel(b, unprojected, 2)); in project_src()
119 nir_channel(b, projected, 0), in project_src()
120 nir_channel(b, unprojected, 1)); in project_src()
174 offset_coord = nir_vec2(b, nir_channel(b, offset_coord, 0), in lower_offset()
[all …]
|
| D | nir_lower_alu_to_scalar.c | 186 return nir_pack_half_2x16_split(b, nir_channel(b, src_vec2, 0), in lower_alu_instr_scalar()
187 nir_channel(b, src_vec2, 1)); in lower_alu_instr_scalar()
224 return nir_ior(b, nir_ishl(b, nir_channel(b, word, 1), in lower_alu_instr_scalar()
226 nir_channel(b, word, 0)); in lower_alu_instr_scalar()
235 return nir_ior(b, nir_ior(b, nir_ishl(b, nir_channel(b, byte, 3), in lower_alu_instr_scalar()
237 nir_ishl(b, nir_channel(b, byte, 2), in lower_alu_instr_scalar()
239 nir_ior(b, nir_ishl(b, nir_channel(b, byte, 1), in lower_alu_instr_scalar()
241 nir_channel(b, byte, 0))); in lower_alu_instr_scalar()
250 sum[i] = nir_fmul(b, nir_channel(b, src0_vec, i), in lower_alu_instr_scalar()
251 nir_channel(b, src1_vec, i)); in lower_alu_instr_scalar()
[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 | 305 nir_channel(b, local_size, 0)); in lower_compute_system_value_instr()
307 nir_channel(b, local_size, 0)), in lower_compute_system_value_instr()
308 nir_channel(b, local_size, 1)); in lower_compute_system_value_instr()
310 nir_imul(b, nir_channel(b, local_size, 0), in lower_compute_system_value_instr()
311 nir_channel(b, local_size, 1))); in lower_compute_system_value_instr()
320 nir_ssa_def *x = nir_channel(b, ids, 0); in lower_compute_system_value_instr()
321 nir_ssa_def *y = nir_channel(b, ids, 1); in lower_compute_system_value_instr()
322 nir_ssa_def *z = nir_channel(b, ids, 2); in lower_compute_system_value_instr()
327 size_x_imm = nir_channel(b, nir_load_workgroup_size(b), 0); in lower_compute_system_value_instr()
417 index = nir_imul(b, nir_channel(b, local_id, 2), in lower_compute_system_value_instr()
[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()
|
| 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_fragcoord_wtrans.c | 62 nir_channel(b, &intr->dest.ssa, 0), in lower_fragcoord_wtrans_impl()
63 nir_channel(b, &intr->dest.ssa, 1), in lower_fragcoord_wtrans_impl()
64 nir_channel(b, &intr->dest.ssa, 2), in lower_fragcoord_wtrans_impl()
65 nir_frcp(b, nir_channel(b, &intr->dest.ssa, 3))); in lower_fragcoord_wtrans_impl()
|
| D | nir_lower_interpolation.c | 114 val = nir_ffma(b, nir_channel(b, bary, 1), in nir_lower_interpolation_block()
115 nir_channel(b, iid, 1), in nir_lower_interpolation_block()
116 nir_channel(b, iid, 0)); in nir_lower_interpolation_block()
117 val = nir_ffma(b, nir_channel(b, bary, 0), in nir_lower_interpolation_block()
118 nir_channel(b, iid, 2), in nir_lower_interpolation_block()
|
| D | nir_lower_viewport_transform.c | 76 nir_ssa_def *w_recip = nir_frcp(&b, nir_channel(&b, input_point, 3)); in nir_lower_viewport_transform()
92 nir_channel(&b, screen, 0), in nir_lower_viewport_transform()
93 nir_channel(&b, screen, 1), in nir_lower_viewport_transform()
94 nir_channel(&b, screen, 2), in nir_lower_viewport_transform()
|
| D | nir_convert_ycbcr.c | 122 chroma_range(b, nir_channel(b, raw_channels, 0), bpcs[0], range), in nir_convert_ycbcr_to_rgb()
123 y_range(b, nir_channel(b, raw_channels, 1), bpcs[1], range), in nir_convert_ycbcr_to_rgb()
124 chroma_range(b, nir_channel(b, raw_channels, 2), bpcs[2], range), in nir_convert_ycbcr_to_rgb()
125 nir_channel(b, raw_channels, 3)); in nir_convert_ycbcr_to_rgb()
141 converted_channels[2], nir_channel(b, raw_channels, 3)); in nir_convert_ycbcr_to_rgb()
|
| /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()
176 nir_ssa_def *tmp = nir_fsat(b, nir_fadd(b, nir_channel(b, lw, 1), in nir_lower_aaline_block()
177 nir_fneg(b, nir_fabs(b, nir_channel(b, lw, 0))))); in nir_lower_aaline_block()
178 nir_ssa_def *tmp1 = nir_fsat(b, nir_fadd(b, nir_channel(b, lw, 3), in nir_lower_aaline_block()
179 nir_fneg(b, nir_fabs(b, nir_channel(b, lw, 2))))); in nir_lower_aaline_block()
182 tmp = nir_fmul(b, nir_channel(b, out_input, 3), tmp); in nir_lower_aaline_block()
184 nir_ssa_def *out = nir_vec4(b, nir_channel(b, out_input, 0), in nir_lower_aaline_block()
185 nir_channel(b, out_input, 1), in nir_lower_aaline_block()
186 nir_channel(b, out_input, 2), in nir_lower_aaline_block()
271 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/radeonsi/ |
| D | si_shaderlib_nir.c | 72 nir_ssa_def *src_dcc_offset = nir_channel(&b, user_sgprs, 0); in si_create_dcc_retile_cs()
75 unpack_2x16(&b, nir_channel(&b, user_sgprs, 1), &src_dcc_pitch, &src_dcc_height); in si_create_dcc_retile_cs()
76 unpack_2x16(&b, nir_channel(&b, user_sgprs, 2), &dst_dcc_pitch, &dst_dcc_height); in si_create_dcc_retile_cs()
89 nir_channel(&b, coord, 0), nir_channel(&b, coord, 1), /* x, y */ in si_create_dcc_retile_cs()
97 nir_channel(&b, coord, 0), nir_channel(&b, coord, 1), /* x, y */ in si_create_dcc_retile_cs()
119 unpack_2x16(&b, nir_channel(&b, user_sgprs, 0), &dcc_pitch, &dcc_height); in gfx9_create_clear_dcc_msaa_cs()
120 unpack_2x16(&b, nir_channel(&b, user_sgprs, 1), &clear_value, &pipe_xor); in gfx9_create_clear_dcc_msaa_cs()
137 nir_channel(&b, coord, 0), nir_channel(&b, coord, 1), /* x, y */ in gfx9_create_clear_dcc_msaa_cs()
138 … tex->buffer.b.b.array_size > 1 ? nir_channel(&b, coord, 2) : zero, /* z */ in gfx9_create_clear_dcc_msaa_cs()
|
| /third_party/mesa3d/src/panfrost/util/ |
| D | pan_lower_framebuffer.c | 156 replicated[i] = nir_channel(b, v, i % num_components); in pan_replicate()
190 nir_unpack_32_2x16(b, nir_channel(b, pack, i >> 1)); in pan_unpack_pure_16()
192 unpacked[i + 0] = nir_channel(b, halves, 0); in pan_unpack_pure_16()
193 unpacked[i + 1] = nir_channel(b, halves, 1); in pan_unpack_pure_16()
244 nir_ssa_def *unpacked = nir_unpack_32_4x8(b, nir_channel(b, pack, 0)); in pan_unpack_pure_8()
315 nir_ishl(b, nir_channel(b, bottom2, 0), nir_imm_int(b, 24 + 0)), in pan_pack_unorm_1010102()
316 nir_ishl(b, nir_channel(b, bottom2, 1), nir_imm_int(b, 24 + 2))), in pan_pack_unorm_1010102()
318 nir_ishl(b, nir_channel(b, bottom2, 2), nir_imm_int(b, 24 + 4)), in pan_pack_unorm_1010102()
319 nir_ishl(b, nir_channel(b, bottom2, 3), nir_imm_int(b, 24 + 6)))); in pan_pack_unorm_1010102()
342 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_tess_io.cpp | 76 return r600_umad_24(b, nir_channel(b, param_base, 0), in r600_tcs_base_address()
78 nir_channel(b, param_base, 3)); in r600_tcs_base_address()
86 nir_channel(b, base, 0), in emil_lsd_in_addr()
91 addr = r600_umad_24(b, nir_channel(b, base, 1), in emil_lsd_in_addr()
107 nir_ssa_def *addr1 = r600_umad_24(b, nir_channel(b, base, 0), in emil_lsd_out_addr()
109 nir_channel(b, base, 2)); in emil_lsd_out_addr()
110 nir_ssa_def *addr2 = r600_umad_24(b, nir_channel(b, base, 1), in emil_lsd_out_addr()
221 remix[i] = nir_channel(b, new_load, chan++); in replace_load_instr()
316 vertices_in = nir_channel(b, load_in_param_base, 2); in r600_lower_tess_io_impl()
319 vertices_in = nir_channel(b, base, 2); in r600_lower_tess_io_impl()
[all …]
|
| D | sfn_instruction_tex.cpp | 152 corr = nir_vec3(b, nir_channel(b, corr2, 0), nir_channel(b, corr2, 1), in lower_coord_shift_normalized()
153 nir_channel( in lower_coord_shift_normalized()
174 corr = nir_vec3(b, nir_channel(b, corr2, 0), nir_channel(b, corr2, 1), in lower_coord_shift_unnormalized()
175 nir_channel(b, tex->src[coord_index].src.ssa, 2)); in lower_coord_shift_unnormalized()
370 nir_vec2(b, nir_channel(b, cubed, 1), nir_channel(b, cubed, 0)), in r600_nir_lower_cube_to_2darray_impl()
371 nir_frcp(b, nir_fabs(b, nir_channel(b, cubed, 2))), in r600_nir_lower_cube_to_2darray_impl()
374 nir_ssa_def *z = nir_channel(b, cubed, 3); in r600_nir_lower_cube_to_2darray_impl()
376 auto slice = nir_fround_even(b, nir_channel(b, tex->src[coord_idx].src.ssa, 3)); in r600_nir_lower_cube_to_2darray_impl()
392 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_64bit.cpp | 177 return nir_vec3(b, nir_channel(b, load1, 0), in merge_64bit_loads()
178 nir_channel(b, load1, 1), in merge_64bit_loads()
179 nir_channel(b, load2, 0)); in merge_64bit_loads()
181 return nir_vec4(b, nir_channel(b, load1, 0), in merge_64bit_loads()
182 nir_channel(b, load1, 1), in merge_64bit_loads()
183 nir_channel(b, load2, 0), in merge_64bit_loads()
184 nir_channel(b, load2, 1)); in merge_64bit_loads()
266 nir_build_store_deref(b, &deref_array2->dest.ssa, nir_channel(b, intr->src[1].ssa, 2), 1); in split_store_deref_array()
290 nir_build_store_deref(b, &deref2->dest.ssa, nir_channel(b, intr->src[1].ssa, 2), 1); in split_store_deref_var()
418 return nir_vec3(b, nir_channel(b, &intr->dest.ssa, 0), in split_double_load_uniform()
[all …]
|
| D | sfn_nir_legalize_image_load_store.cpp | 97 … case 2: in_range = nir_iand(b, nir_channel(b, in_range, 0), nir_channel(b, in_range, 1)); break; in r600_legalize_image_load_store_impl()
99 auto tmp = nir_iand(b, nir_channel(b, in_range, 0), nir_channel(b, in_range, 1)); in r600_legalize_image_load_store_impl()
100 in_range = nir_iand(b, tmp, nir_channel(b, in_range, 2)); in r600_legalize_image_load_store_impl()
|
| /third_party/mesa3d/src/gallium/drivers/d3d12/ |
| 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/compiler/nir/tests/ |
| D | comparison_pre_tests.cpp | 97 nir_ssa_def *a = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
149 nir_ssa_def *b = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
202 nir_ssa_def *a = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
254 nir_ssa_def *b = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
307 nir_ssa_def *a = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
360 nir_ssa_def *a = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
414 nir_ssa_def *a = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
467 nir_ssa_def *a = nir_channel(&bld, nir_fadd(&bld, v1, v3), 0); in TEST_F()
|