| /third_party/mesa3d/src/gallium/drivers/r600/sfn/ |
| D | sfn_nir_lower_tex.cpp | 43 auto corr2 = nir_fadd(b, nir_channels(b, tex->src[coord_index].src.ssa, 3), in lower_coord_shift_normalized()
65 auto corr2 = nir_fadd(b, nir_channels(b, tex->src[coord_index].src.ssa, 3), in lower_coord_shift_unnormalized()
171 scale = nir_frcp(b, nir_channels(b, size, 1)); in lower_txl_txf_array_or_cube()
175 scale = nir_frcp(b, nir_channels(b, size, in lower_txl_txf_array_or_cube()
261 auto cubed = nir_cube_r600(b, nir_channels(b, tex->src[coord_idx].src.ssa, 0x7)); in r600_nir_lower_cube_to_2darray_impl()
|
| D | sfn_nir_lower_64bit.cpp | 210 return nir_fneu(b, nir_channels(b, nir_ssa_for_alu_src(b, alu, 0), mask), in lower()
440 auto src_xy = nir_channels(b, intr->src[1].ssa, 3); in split_store_deref_array()
455 nir_build_store_deref(b, &deref_array2->dest.ssa, nir_channels(b, intr->src[1].ssa, 0xc), 3); in split_store_deref_array()
468 auto src_xy = nir_channels(b, intr->src[1].ssa, 3); in split_store_deref_var()
479 nir_build_store_deref(b, &deref2->dest.ssa, nir_channels(b, intr->src[1].ssa, 0xc), 3); in split_store_deref_var()
567 auto src1 = nir_channels(b, src.ssa, 3); in split_store_output()
568 auto src2 = nir_channels(b, src.ssa, old_components == 3 ? 4 : 0xc); in split_store_output()
672 src[0][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 2), 3); in split_reduction3()
673 src[0][1] = nir_channels(b, nir_ssa_for_src(b, alu->src[1].src, 2), 3); in split_reduction3()
687 src[0][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 2), 3); in split_reduction4()
[all …]
|
| D | sfn_nir_legalize_image_load_store.cpp | 94 nir_channels(b, ir->src[1].ssa, src1_mask), in r600_legalize_image_load_store_impl()
95 nir_channels(b, img_size, mask)); in r600_legalize_image_load_store_impl()
|
| /third_party/mesa3d/src/gallium/drivers/d3d12/ |
| D | d3d12_lower_image_casts.c | 76 packed_channels[0] = nir_pack_unorm_2x16(b, nir_channels(b, value, 0x3)); in convert_value()
77 packed_channels[1] = nir_pack_unorm_2x16(b, nir_channels(b, value, 0x3 << 2)); in convert_value()
85 packed_channels[0] = nir_pack_snorm_2x16(b, nir_channels(b, value, 0x3)); in convert_value()
86 packed_channels[1] = nir_pack_snorm_2x16(b, nir_channels(b, value, 0x3 << 2)); in convert_value()
|
| /third_party/mesa3d/src/amd/vulkan/ |
| D | radv_meta_dcc_retile.c | 41 nir_ssa_def *src_dcc_pitch = nir_channels(&b, src_dcc_size, 1); in build_dcc_retile_compute_shader()
42 nir_ssa_def *src_dcc_height = nir_channels(&b, src_dcc_size, 2); in build_dcc_retile_compute_shader()
45 nir_ssa_def *dst_dcc_pitch = nir_channels(&b, dst_dcc_size, 1); in build_dcc_retile_compute_shader()
46 nir_ssa_def *dst_dcc_height = nir_channels(&b, dst_dcc_size, 2); in build_dcc_retile_compute_shader()
|
| D | radv_acceleration_structure.c | 1158 nir_ssa_def *node_dst_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst0, 0b0011)); in build_leaf_shader()
1159 nir_ssa_def *scratch_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst0, 0b1100)); in build_leaf_shader()
1167 nir_imul_imm(&b, nir_channels(&b, nir_load_workgroup_id(&b, 32), 1), in build_leaf_shader()
1169 nir_channels(&b, nir_load_local_invocation_id(&b), 1)); in build_leaf_shader()
1184 nir_ssa_def *vertex_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 0b0011)); in build_leaf_shader()
1185 nir_ssa_def *index_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 0b1100)); in build_leaf_shader()
1186 nir_ssa_def *transform_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst3, 3)); in build_leaf_shader()
1267 nir_ssa_def *aabb_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 0b0011)); in build_leaf_shader()
1309 nir_ssa_def *ptr = nir_iadd(&b, nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 0b0011)), in build_leaf_shader()
1317 nir_ssa_def *addr = nir_iadd(&b, nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 0b0011)), in build_leaf_shader()
[all …]
|
| D | radv_meta_buffer.c | 14 nir_ssa_def *buffer_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst, 0b0011)); in build_buffer_fill_shader()
40 nir_ssa_def *src_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst, 0b0011)); in build_buffer_copy_shader()
41 nir_ssa_def *dst_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst, 0b1100)); in build_buffer_copy_shader()
|
| D | radv_meta_etc_decode.c | 200 nir_ssa_def *offset = nir_channels(&b, consts, 7); in build_shader()
255 nir_ssa_def *pixel_coord = nir_iand_imm(&b, nir_channels(&b, coord, 3), 3); in build_shader()
272 nir_bcsel(&b, alpha_bits_8, nir_channels(&b, payload, 0xC), nir_channels(&b, payload, 3)); in build_shader()
297 decode_etc2_alpha(&b, nir_channels(&b, payload, 3), linear_pixel, false, NULL), 1); in build_shader()
493 val[i] = decode_etc2_alpha(&b, nir_channels(&b, payload, 3 << (2 * i)), linear_pixel, true, in build_shader()
|
| /third_party/mesa3d/src/intel/compiler/ |
| D | brw_nir_rt_builder.h | 316 defs->base_mem_addr = nir_pack_64_2x32(b, nir_channels(b, data, 0x3)); in brw_nir_rt_load_globals_addr()
319 nir_pack_64_2x32(b, nir_channels(b, data, 0x3 << 2)); in brw_nir_rt_load_globals_addr()
336 defs->launch_size = nir_channels(b, data, 0x7u << 13); in brw_nir_rt_load_globals_addr()
347 nir_pack_64_2x32(b, nir_channels(b, data, 0x3 << 2)); in brw_nir_rt_load_globals_addr()
419 defs->tri_bary = nir_channels(b, data, 0x6); in brw_nir_rt_load_mem_hit_from_addr()
433 brw_nir_rt_unpack_leaf_ptr(b, nir_channels(b, data, 0x3 << 0)); in brw_nir_rt_load_mem_hit_from_addr()
435 brw_nir_rt_unpack_leaf_ptr(b, nir_channels(b, data, 0x3 << 2)); in brw_nir_rt_load_mem_hit_from_addr()
799 defs->orig = nir_channels(b, data[0], 0x7); in brw_nir_rt_load_mem_ray_from_addr()
|
| D | brw_nir_lower_storage_image.c | 120 nir_channels(b, coord, 0x3); in image_address()
157 nir_channels(b, stride, 0xc))); in image_address()
178 nir_channels(b, tiling, 0x3)); in image_address()
179 nir_ssa_def *major = nir_ushr(b, xypos, nir_channels(b, tiling, 0x3)); in image_address()
|
| /third_party/mesa3d/src/compiler/nir/ |
| D | nir_lower_ubo_vec4.c | 146 nir_channels(b, result, high_channels), in nir_lower_ubo_vec4_lower()
147 nir_channels(b, result, low_channels)); in nir_lower_ubo_vec4_lower()
|
| D | nir_lower_drawpixels.c | 156 nir_src_for_ssa(nir_channels(b, texcoord, in lower_color()
197 tex->src[2].src = nir_src_for_ssa(nir_channels(b, def, 0x3)); in lower_color()
211 tex->src[0].src = nir_src_for_ssa(nir_channels(b, def, 0xc)); in lower_color()
|
| D | nir_split_64bit_vec3_and_vec4.c | 210 nir_ssa_def *src_xy = nir_channels(b, intr->src[1].ssa, 3); in split_store_deref()
216 nir_ssa_def *src_zw = nir_channels(b, intr->src[1].ssa, write_mask_zw); in split_store_deref()
253 nir_ssa_def *new_src = nir_channels(b, src->src.ssa, in split_phi()
|
| D | nir_lower_fb_read.c | 65 tex->src[0].src = nir_src_for_ssa(nir_channels(b, fragcoord, 0x3)); in lower_fb_read()
|
| D | nir_lower_viewport_transform.c | 79 nir_channels(&b, input_point, 0x7), w_recip); in nir_lower_viewport_transform()
|
| D | nir_lower_bitmap.c | 105 nir_src_for_ssa(nir_channels(b, texcoord, in lower_bitmap()
|
| /third_party/mesa3d/src/panfrost/util/ |
| D | pan_lower_framebuffer.c | 124 return nir_channels(b, pack, (1 << num_components) - 1); in pan_unpack_pure_32()
135 nir_ssa_def *lo = nir_pack_32_2x16(b, nir_channels(b, v4, 0x3 << 0)); in pan_pack_pure_16()
136 nir_ssa_def *hi = nir_pack_32_2x16(b, nir_channels(b, v4, 0x3 << 2)); in pan_pack_pure_16()
205 return nir_channels(b, unpacked, (1 << num_components) - 1); in pan_unpack_pure_8()
358 nir_ssa_def *rgb = nir_channels(b, linear, 0x7); in pan_linear_to_srgb()
|
| D | pan_lower_xfb.c | 59 nir_ssa_def *value = nir_channels(b, src, BITFIELD_MASK(num_components) << start_component); in lower_xfb_output()
|
| /third_party/mesa3d/src/gallium/drivers/radeonsi/ |
| D | si_shaderlib_nir.c | 62 nir_ssa_def *local_ids = nir_channels(b, nir_load_local_invocation_id(b), mask); in get_global_ids()
63 nir_ssa_def *block_ids = nir_channels(b, nir_load_workgroup_id(b, 32), mask); in get_global_ids()
64 nir_ssa_def *block_size = nir_channels(b, nir_load_workgroup_size(b), mask); in get_global_ids()
212 nir_channels(&b, nir_imm_ivec4(&b, tex->surface.u.gfx9.color.dcc_block_width, in gfx9_create_clear_dcc_msaa_cs()
|
| /third_party/mesa3d/src/gallium/drivers/zink/ |
| D | zink_lower_cubemap_to_array.c | 171 … nir_ssa_def *c = nir_channels(b, psrc->ssa, BITFIELD_MASK(nir_tex_instr_src_size(array_tex, s))); in create_array_tex_from_cube_tex()
312 nir_ssa_def *texel_coords = nir_fmul(b, nir_channels(b, coord, 3), in handle_cube_gather()
313 nir_i2f32(b, nir_channels(b, tex_size, 3))); in handle_cube_gather()
492 return nir_channels(b, size, BITFIELD_MASK(num_components)); in lower_cube_txs()
|
| /third_party/mesa3d/src/microsoft/compiler/ |
| D | dxil_nir_lower_int_cubemaps.c | 350 nir_ssa_def *texel_coords = nir_fmul(b, nir_channels(b, coord, 3), in handle_cube_gather()
351 nir_i2f32(b, nir_channels(b, tex_size, 3))); in handle_cube_gather()
455 return nir_channels(b, &tex->dest.ssa, 3); in lower_cube_txs()
469 return nir_channels(b, &intr->dest.ssa, 3); in lower_cube_image_size()
|
| /third_party/mesa3d/src/freedreno/ir3/ |
| D | ir3_nir_lower_load_barycentric_at_offset.c | 77 return nir_fmul(b, nir_channels(b, pos, 0x3), nir_frcp(b, chan(pos, 2))); in ir3_nir_lower_load_barycentric_at_offset_instr()
|
| D | ir3_nir_lower_wide_load_store.c | 65 nir_ssa_def *v = nir_channels(b, val, BITFIELD_MASK(c) << off); in lower_wide_load_store()
|
| /third_party/mesa3d/src/intel/blorp/ |
| D | blorp_nir_builder.h | 56 coord = nir_channels(b, xy_pos, 0x3); in blorp_nir_txf_ms_mcs()
|
| /third_party/mesa3d/src/mesa/state_tracker/ |
| D | st_pbo_compute.c | 406 write_conversion(b, nir_channels(b, pixel, 3), buffer_offset, sd); in grab_components()
415 write_conversion(b, nir_channels(b, pixel, (1 << 2) - 1), buffer_offset, sd); in grab_components()
418 write_conversion(b, nir_channels(b, pixel, (1 << 3) - 1), buffer_offset, sd); in grab_components()
420 write_conversion(b, nir_channels(b, pixel, (1 << 4) - 1), buffer_offset, sd); in grab_components()
536 …pack[1] = nir_format_pack_uint_unmasked_ssa(b, nir_channels(b, pixel, 6), nir_channels(b, sd->bits… in convert_swap_write()
|