| /dports/graphics/libosmesa-gallium/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/lang/clover/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/libosmesa/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/mesa-libs/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/mesa-gallium-xa/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/mesa-dri-gallium/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/mesa-gallium-va/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/mesa-gallium-vdpau/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/graphics/mesa-dri/mesa-21.3.6/src/intel/compiler/ |
| H A 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()
|
| /dports/lang/clover/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/libosmesa/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/libosmesa-gallium/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/mesa-libs/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/mesa-dri-gallium/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/mesa-gallium-va/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/mesa-gallium-vdpau/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/mesa-gallium-xa/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/mesa-dri/mesa-21.3.6/src/gallium/drivers/radeonsi/ |
| H A 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()
|
| /dports/graphics/libosmesa-gallium/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|
| /dports/lang/clover/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|
| /dports/graphics/libosmesa/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|
| /dports/graphics/mesa-libs/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|
| /dports/graphics/mesa-gallium-xa/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|
| /dports/graphics/mesa-gallium-va/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|
| /dports/graphics/mesa-dri-gallium/mesa-21.3.6/src/gallium/drivers/r600/sfn/ |
| H A D | sfn_nir_lower_64bit.cpp | 253 auto src_xy = nir_channels(b, intr->src[1].ssa, 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()
503 src[1][0] = nir_channels(b, nir_ssa_for_src(b, alu->src[0].src, 4), 0xc); in split_reduction4()
[all …]
|