| /third_party/mesa3d/src/intel/compiler/ |
| D | brw_nir_rt_builder.h | 215 defs->base_mem_addr = nir_pack_64_2x32(b, nir_channels(b, data, 0x3)); in brw_nir_rt_load_globals()
218 nir_pack_64_2x32(b, nir_channels(b, data, 0x3 << 2)); in brw_nir_rt_load_globals()
235 defs->launch_size = nir_channels(b, data, 0x7u << 13); in brw_nir_rt_load_globals()
247 nir_pack_64_2x32(b, nir_channels(b, data, 0x3 << 2)); in brw_nir_rt_load_globals()
288 defs->tri_bary = nir_channels(b, data, 0x6); in brw_nir_rt_load_mem_hit()
298 brw_nir_rt_unpack_leaf_ptr(b, nir_channels(b, data, 0x3 << 0)); in brw_nir_rt_load_mem_hit()
300 brw_nir_rt_unpack_leaf_ptr(b, nir_channels(b, data, 0x3 << 2)); in brw_nir_rt_load_mem_hit()
426 defs->orig = nir_channels(b, data[0], 0x7); in brw_nir_rt_load_mem_ray()
|
| D | brw_nir_lower_storage_image.c | 103 coord = nir_channels(b, coord, (1 << dims) - 1); in image_address()
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()
460 color = nir_channels(b, color, (1 << image.chans) - 1); in convert_color_for_store()
|
| /third_party/mesa3d/src/gallium/drivers/radeonsi/ |
| D | si_shaderlib_nir.c | 44 nir_ssa_def *local_ids = nir_channels(b, nir_load_local_invocation_id(b), mask); in get_global_ids()
45 nir_ssa_def *block_ids = nir_channels(b, nir_load_workgroup_id(b, 32), mask); in get_global_ids()
46 nir_ssa_def *block_size = nir_channels(b, nir_load_workgroup_size(b), mask); in get_global_ids()
129 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/r600/sfn/ |
| D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 3); in split_store_deref_array()
268 nir_build_store_deref(b, &deref_array2->dest.ssa, nir_channels(b, intr->src[1].ssa, 0xc), 3); in split_store_deref_array()
281 auto src_xy = nir_channels(b, intr->src[1].ssa, 3); in split_store_deref_var()
292 nir_build_store_deref(b, &deref2->dest.ssa, nir_channels(b, intr->src[1].ssa, 0xc), 3); in split_store_deref_var()
380 auto src1 = nir_channels(b, src.ssa, 3); in split_store_output()
381 auto src2 = nir_channels(b, src.ssa, old_components == 3 ? 4 : 0xc); in split_store_output()
485 src[0][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 2), 3); in split_reduction3()
486 src[0][1] = nir_channels(b, nir_ssa_for_src(b, alu->src[1].src, 2), 3); in split_reduction3()
500 src[0][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 2), 3); in split_reduction4()
501 src[0][1] = nir_channels(b, nir_ssa_for_src(b, alu->src[1].src, 2), 3); in split_reduction4()
[all …]
|
| D | sfn_instruction_tex.cpp | 150 auto corr2 = nir_fadd(b, nir_channels(b, tex->src[coord_index].src.ssa, 3), in lower_coord_shift_normalized()
172 auto corr2 = nir_fadd(b, nir_channels(b, tex->src[coord_index].src.ssa, 3), in lower_coord_shift_unnormalized()
278 scale = nir_frcp(b, nir_channels(b, size, in lower_txl_txf_array_or_cube()
282 scale = nir_frcp(b, nir_channels(b, size, 1)); in lower_txl_txf_array_or_cube()
368 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_legalize_image_load_store.cpp | 93 nir_channels(b, ir->src[1].ssa, src1_mask), in r600_legalize_image_load_store_impl()
94 nir_channels(b, img_size, mask)); in r600_legalize_image_load_store_impl()
|
| /third_party/mesa3d/src/amd/vulkan/ |
| D | radv_acceleration_structure.c | 935 nir_ssa_def *node_dst_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst0, 3)); in build_leaf_shader()
936 nir_ssa_def *scratch_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst0, 12)); in build_leaf_shader()
943 nir_umul24(&b, nir_channels(&b, nir_load_workgroup_id(&b, 32), 1), in build_leaf_shader()
945 nir_channels(&b, nir_load_local_invocation_id(&b), 1)); in build_leaf_shader()
952 nir_ssa_def *vertex_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 3)); in build_leaf_shader()
953 nir_ssa_def *index_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 12)); in build_leaf_shader()
954 nir_ssa_def *transform_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst3, 3)); in build_leaf_shader()
1025 nir_ssa_def *aabb_addr = nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 3)); in build_leaf_shader()
1068 nir_ssa_def *ptr = nir_iadd(&b, nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 3)), in build_leaf_shader()
1076 nir_ssa_def *addr = nir_iadd(&b, nir_pack_64_2x32(&b, nir_channels(&b, pconst2, 3)), in build_leaf_shader()
[all …]
|
| D | radv_meta_dcc_retile.c | 42 nir_ssa_def *src_dcc_pitch = nir_channels(&b, src_dcc_size, 1); in build_dcc_retile_compute_shader()
43 nir_ssa_def *src_dcc_height = nir_channels(&b, src_dcc_size, 2); in build_dcc_retile_compute_shader()
46 nir_ssa_def *dst_dcc_pitch = nir_channels(&b, dst_dcc_size, 1); in build_dcc_retile_compute_shader()
47 nir_ssa_def *dst_dcc_height = nir_channels(&b, dst_dcc_size, 2); in build_dcc_retile_compute_shader()
|
| D | radv_meta.c | 692 return nir_channels(b, rsrc, 0x3); in radv_meta_load_descriptor()
700 nir_ssa_def *local_ids = nir_channels(b, nir_load_local_invocation_id(b), mask); in get_global_ids()
701 nir_ssa_def *block_ids = nir_channels(b, nir_load_workgroup_id(b, 32), mask); in get_global_ids()
702 nir_ssa_def *block_size = nir_channels( in get_global_ids()
|
| D | radv_meta_resolve_fs.c | 65 nir_ssa_def *pos_in = nir_channels(&b, nir_load_frag_coord(&b), 0x3); in build_resolve_fragment_shader()
70 nir_ssa_def *img_coord = nir_channels(&b, nir_iadd(&b, pos_int, src_offset), 0x3); in build_resolve_fragment_shader()
343 nir_ssa_def *pos_in = nir_channels(&b, nir_load_frag_coord(&b), 0x3); in build_depth_stencil_resolve_fragment_shader()
347 nir_ssa_def *img_coord = nir_channels(&b, pos_int, 0x3); in build_depth_stencil_resolve_fragment_shader()
|
| /third_party/mesa3d/src/compiler/nir/ |
| D | nir_lower_ubo_vec4.c | 147 nir_channels(b, result, high_channels), in nir_lower_ubo_vec4_lower()
148 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_lower_readonly_images_to_tex.c | 149 nir_channels(b, intrin->src[1].ssa, in lower_readonly_image_op()
189 res = nir_channels(b, res, (1 << num_components) - 1); in lower_readonly_image_op()
|
| D | nir_opt_shrink_vectors.c | 186 nir_ssa_def *data = nir_channels(b, instr->src[3].ssa, BITSET_MASK(components)); in opt_shrink_vectors_image_store()
243 nir_ssa_def *def = nir_channels(b, instr->src[0].ssa, in opt_shrink_vectors_intrinsic()
|
| 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()
|
| D | nir_lower_vec3_to_vec4.c | 78 nir_ssa_def *vec3 = nir_channels(&b, &intrin->dest.ssa, 0x7); in lower_vec3_to_vec4_impl()
|
| D | nir_lower_wrmasks.c | 120 value = nir_channels(b, value, cur_mask); in split_wrmask()
|
| /third_party/mesa3d/src/panfrost/util/ |
| D | pan_lower_framebuffer.c | 164 return nir_channels(b, pack, (1 << num_components) - 1); in pan_unpack_pure_32()
175 nir_ssa_def *lo = nir_pack_32_2x16(b, nir_channels(b, v4, 0x3 << 0)); in pan_pack_pure_16()
176 nir_ssa_def *hi = nir_pack_32_2x16(b, nir_channels(b, v4, 0x3 << 2)); in pan_pack_pure_16()
245 return nir_channels(b, unpacked, (1 << num_components) - 1); in pan_unpack_pure_8()
398 nir_ssa_def *rgb = nir_channels(b, linear, 0x7); in pan_linear_to_srgb()
|
| /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/microsoft/compiler/ |
| D | dxil_nir_lower_int_samplers.c | 81 nir_ssa_def *ssa_src = nir_channels(b, tex->src[coord_index].src.ssa, in dx_get_texture_lod()
464 nir_ssa_def *coord = nir_fmul(b, nir_channels(b, params.size, mask), in lower_sample_to_txf_for_integer_tex_impl()
465 nir_channels(b, old_coord, mask)); in lower_sample_to_txf_for_integer_tex_impl()
|
| /third_party/mesa3d/src/mesa/state_tracker/ |
| D | st_pbo.c | 469 nir_iadd(&b, nir_channels(&b, param, TGSI_WRITEMASK_XY), in create_fs()
470 nir_f2i32(&b, nir_channels(&b, coord, TGSI_WRITEMASK_XY))); in create_fs()
485 texcoord = nir_f2i32(&b, nir_channels(&b, coord, TGSI_WRITEMASK_XY)); in create_fs()
|
| /third_party/mesa3d/src/gallium/drivers/asahi/ |
| D | agx_blit.c | 43 nir_ssa_def *coord = nir_channels(&b, fragcoord, 0x3); in agx_build_reload_shader()
|
| /third_party/mesa3d/src/broadcom/compiler/ |
| D | v3d_nir_lower_image_load_store.c | 98 nir_ssa_def *color = nir_channels(b, in v3d_nir_lower_image_store()
|