Home
last modified time | relevance | path

Searched refs:nir_channels (Results 1 - 25 of 67) sorted by relevance

123

/third_party/mesa3d/src/gallium/drivers/r600/sfn/
H A Dsfn_nir_lower_tex.cpp43 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()
H A Dsfn_nir_legalize_image_load_store.cpp94 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()
H A Dsfn_nir_lower_64bit.cpp210 return nir_fneu(b, nir_channels(b, nir_ssa_for_alu_src(b, alu, 0), mask),
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( in split_reduction4()
[all...]
/third_party/mesa3d/src/gallium/drivers/d3d12/
H A Dd3d12_lower_image_casts.c76 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/compiler/nir/
H A Dnir_lower_ubo_vec4.c146 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()
H A Dnir_split_64bit_vec3_and_vec4.c210 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()
H A Dnir_lower_drawpixels.c156 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()
H A Dnir_lower_viewport_transform.c79 nir_channels(&b, input_point, 0x7), w_recip); in nir_lower_viewport_transform()
H A Dnir_lower_fb_read.c65 tex->src[0].src = nir_src_for_ssa(nir_channels(b, fragcoord, 0x3)); in lower_fb_read()
H A Dnir_lower_wrmasks.c120 value = nir_channels(b, value, cur_mask); in split_wrmask()
H A Dnir_lower_vec3_to_vec4.c78 nir_ssa_def *vec3 = nir_channels(&b, &intrin->dest.ssa, 0x7); in lower_vec3_to_vec4_impl()
H A Dnir_lower_bitmap.c105 nir_src_for_ssa(nir_channels(b, texcoord, in lower_bitmap()
/third_party/mesa3d/src/amd/vulkan/
H A Dradv_acceleration_structure.c1158 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( in build_leaf_shader()
[all...]
H A Dradv_meta_dcc_retile.c41 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()
H A Dradv_meta_buffer.c14 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()
H A Dradv_meta_etc_decode.c200 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/panfrost/util/
H A Dpan_lower_framebuffer.c124 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()
/third_party/mesa3d/src/gallium/drivers/radeonsi/
H A Dsi_shaderlib_nir.c62 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/intel/compiler/
H A Dbrw_nir_rt_builder.h316 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()
H A Dbrw_nir_lower_storage_image.c120 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/freedreno/ir3/
H A Dir3_nir_lower_load_barycentric_at_offset.c77 return nir_fmul(b, nir_channels(b, pos, 0x3), nir_frcp(b, chan(pos, 2))); in ir3_nir_lower_load_barycentric_at_offset_instr()
H A Dir3_nir_lower_wide_load_store.c65 nir_ssa_def *v = nir_channels(b, val, BITFIELD_MASK(c) << off); in lower_wide_load_store()
/third_party/mesa3d/src/gallium/drivers/zink/
H A Dzink_lower_cubemap_to_array.c171 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/
H A Ddxil_nir_lower_int_cubemaps.c350 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()
H A Ddxil_nir_lower_int_samplers.c81 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()

Completed in 23 milliseconds

123