Search

Home

Sort by

Full Search
Definition
Symbol
File Path
History
Type

In Project(s)

Searched refs:intrin (Results 1 - 25 of 218) sorted by relevance

12 3 4 5 6 7 8 9

/xsrc/external/mit/MesaLib/dist/src/compiler/nir/
H A D	nir_lower_image.c	35 lower_cube_size(nir_builder b, nir_intrinsic_instr intrin) argument 37 assert(nir_intrinsic_image_dim(intrin) == GLSL_SAMPLER_DIM_CUBE); 39 b->cursor = nir_before_instr(&intrin->instr); 42 nir_instr_as_intrinsic(nir_instr_clone(b->shader, &intrin->instr)); 49 unsigned coord_comps = intrin->dest.ssa.num_components; 58 nir_ssa_def vec = nir_vec(b, comps, intrin->dest.ssa.num_components); 59 nir_ssa_def_rewrite_uses(&intrin->dest.ssa, vec); 60 nir_instr_remove(&intrin->instr); 61 nir_instr_free(&intrin->instr); 71 nir_intrinsic_instr intrin local in function:lower_image_instr [all...]
H A D	nir_lower_vec3_to_vec4.c	63 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_vec3_to_vec4_impl 64 switch (intrin->intrinsic) { 66 if (intrin->num_components != 3) 69 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 73 assert(intrin->dest.is_ssa); 74 intrin->num_components = 4; 75 intrin->dest.ssa.num_components = 4; 77 b.cursor = nir_after_instr(&intrin->instr); 78 nir_ssa_def *vec3 = nir_channels(&b, &intrin->dest.ssa, 0x7); 79 nir_ssa_def_rewrite_uses_after(&intrin [all...]
H A D	nir_gs_count_vertices.c	33 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:as_intrinsic 34 if (intrin->intrinsic != op) 37 return intrin; 78 nir_intrinsic_instr intrin = as_set_vertex_and_primitive_count(instr); local in function:nir_gs_count_vertices_and_primitives 79 if (!intrin) 82 unsigned stream = nir_intrinsic_stream_id(intrin); 92 if (nir_src_is_const(intrin->src[0])) 93 vtxcnt = nir_src_as_int(intrin->src[0]); 94 if (nir_src_is_const(intrin->src[1])) 95 prmcnt = nir_src_as_int(intrin [all...]
H A D	nir_lower_array_deref_of_vec.c	76 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_array_deref_of_vec_impl 77 assert(intrin->intrinsic != nir_intrinsic_copy_deref); 79 if (intrin->intrinsic != nir_intrinsic_load_deref && 80 intrin->intrinsic != nir_intrinsic_interp_deref_at_centroid && 81 intrin->intrinsic != nir_intrinsic_interp_deref_at_sample && 82 intrin->intrinsic != nir_intrinsic_interp_deref_at_offset && 83 intrin->intrinsic != nir_intrinsic_interp_deref_at_vertex && 84 intrin->intrinsic != nir_intrinsic_store_deref) 87 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 103 assert(intrin [all...]
H A D	nir_opt_uniform_atomics.c	46 #define OP_NOIMG(intrin, alu) \ 47 case nir_intrinsic_ssbo_atomic_##intrin: \ 51 case nir_intrinsic_shared_atomic_##intrin: \ 52 case nir_intrinsic_global_atomic_##intrin: \ 53 case nir_intrinsic_deref_atomic_##intrin: \ 57 #define OP(intrin, alu) \ 58 OP_NOIMG(intrin, alu) \ 59 case nir_intrinsic_image_deref_atomic_##intrin: \ 60 case nir_intrinsic_image_atomic_##intrin: \ 61 case nir_intrinsic_bindless_image_atomic_##intrin 90 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(scalar.def->parent_instr); local in function:get_dim 141 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(scalar.def->parent_instr); local in function:match_invocation_comparison 195 optimize_atomic(nir_builder * b,nir_intrinsic_instr * intrin,bool return_prev) argument 236 optimize_and_rewrite_atomic(nir_builder * b,nir_intrinsic_instr * intrin) argument 281 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:opt_uniform_atomics [all...]
H A D	nir_opt_dead_write_vars.c	50 nir_intrinsic_instr intrin; member in struct:write_entry 75 nir_intrinsic_instr intrin, 92 nir_instr_remove(&entry->intrin->instr); 101 .intrin = intrin, 133 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:remove_dead_write_vars_local 134 switch (intrin->intrinsic) { 159 if (nir_intrinsic_memory_semantics(intrin) & NIR_MEMORY_RELEASE) { 161 nir_intrinsic_memory_modes(intrin)); 175 nir_deref_instr src = nir_src_as_deref(intrin 74 update_unused_writes(struct util_dynarray * unused_writes,nir_intrinsic_instr * intrin,nir_deref_instr * dst,nir_component_mask_t mask) argument [all...]
H A D	nir_lower_subgroups.c	33 lower_subgroups_64bit_split_intrinsic(nir_builder b, nir_intrinsic_instr intrin, argument 38 comp = nir_unpack_64_2x32_split_x(b, intrin->src[0].ssa); 40 comp = nir_unpack_64_2x32_split_y(b, intrin->src[0].ssa); 42 nir_intrinsic_instr intr = nir_intrinsic_instr_create(b->shader, intrin->intrinsic); 44 intr->const_index[0] = intrin->const_index[0]; 45 intr->const_index[1] = intrin->const_index[1]; 47 if (nir_intrinsic_infos[intrin->intrinsic].num_srcs == 2) 48 nir_src_copy(&intr->src[1], &intrin->src[1]); 56 lower_subgroup_op_to_32bit(nir_builder b, nir_intrinsic_instr intrin) argument 58 assert(intrin 107 lower_subgroup_op_to_scalar(nir_builder b,nir_intrinsic_instr * intrin,bool lower_to_32bit) argument 147 lower_vote_eq_to_scalar(nir_builder * b,nir_intrinsic_instr * intrin) argument 173 lower_vote_eq(nir_builder * b,nir_intrinsic_instr * intrin) argument 201 lower_shuffle_to_swizzle(nir_builder * b,nir_intrinsic_instr * intrin,const nir_lower_subgroups_options * options) argument 229 lower_shuffle(nir_builder * b,nir_intrinsic_instr * intrin,const nir_lower_subgroups_options * options) argument 478 lower_dynamic_quad_broadcast(nir_builder * b,nir_intrinsic_instr * intrin,const nir_lower_subgroups_options * options) argument 518 lower_read_invocation_to_cond(nir_builder * b,nir_intrinsic_instr * intrin) argument 531 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:lower_subgroups_instr [all...]
H A D	nir_opt_fragdepth.c	42 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:ssa_def_is_source_depth 43 if (intrin->intrinsic != nir_intrinsic_load_frag_coord) 65 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_opt_fragdepth 66 if (intrin->intrinsic != nir_intrinsic_store_deref) 69 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 82 if (ssa_def_is_source_depth(intrin->src[1].ssa)) { 84 intrin so we can try to remove it later. */ 85 store_intrin = intrin;
H A D	nir_opt_constant_folding.c	`182 try_fold_intrinsic(nir_builder b, nir_intrinsic_instr intrin, argument 185 switch (intrin->intrinsic) { 189 if (nir_src_is_const(intrin->src[0])) { 190 if (nir_src_as_bool(intrin->src[0])) { 191 b->cursor = nir_before_instr(&intrin->instr); 193 switch (intrin->intrinsic) { 210 nir_instr_remove(&intrin->instr); 216 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 219 b->cursor = nir_before_instr(&intrin->instr); 220 nir_ssa_def val = nir_build_imm(b, intrin [all...]`
H A D	nir_lower_scratch.c	39 nir_intrinsic_instr intrin, 42 b->cursor = nir_before_instr(&intrin->instr); 44 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 54 if (intrin->intrinsic == nir_intrinsic_load_deref) { 55 unsigned bit_size = intrin->dest.ssa.bit_size; 57 b, intrin->num_components, bit_size == 1 ? 32 : bit_size, offset, .align_mul=align); 61 nir_ssa_def_rewrite_uses(&intrin->dest.ssa, value); 63 assert(intrin->intrinsic == nir_intrinsic_store_deref); 65 assert(intrin->src[1].is_ssa); 66 nir_ssa_def value = intrin 38 lower_load_store(nir_builder b,nir_intrinsic_instr * intrin,glsl_type_size_align_func size_align) argument 89 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(src->parent_instr); local in function:only_used_for_load_store 115 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_vars_to_scratch 199 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_vars_to_scratch [all...]
/xsrc/external/mit/MesaLib.old/dist/src/compiler/nir/
H A D	nir_gs_count_vertices.c	`33 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:as_intrinsic 34 if (intrin->intrinsic != op) 37 return intrin; 69 nir_intrinsic_instr intrin = as_set_vertex_count(instr); local in function:nir_gs_count_vertices 70 if (!intrin) 74 if (!nir_src_is_const(intrin->src[0])) 78 count = nir_src_as_int(intrin->src[0]); 84 if (count != nir_src_as_int(intrin->src[0]))`
H A D	nir_lower_scratch.c	53 nir_intrinsic_instr intrin, 56 b->cursor = nir_before_instr(&intrin->instr); 58 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 68 if (intrin->intrinsic == nir_intrinsic_load_deref) { 71 load->num_components = intrin->num_components; 75 intrin->dest.ssa.num_components, 76 intrin->dest.ssa.bit_size, NULL); 83 nir_ssa_def_rewrite_uses(&intrin->dest.ssa, 86 assert(intrin->intrinsic == nir_intrinsic_store_deref); 88 assert(intrin 52 lower_load_store(nir_builder * b,nir_intrinsic_instr * intrin,glsl_type_size_align_func size_align) argument 122 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_vars_to_scratch 172 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_vars_to_scratch [all...]
H A D	nir_lower_subgroups.c	32 lower_subgroups_64bit_split_intrinsic(nir_builder b, nir_intrinsic_instr intrin, argument 37 comp = nir_unpack_64_2x32_split_x(b, intrin->src[0].ssa); 39 comp = nir_unpack_64_2x32_split_y(b, intrin->src[0].ssa); 41 nir_intrinsic_instr intr = nir_intrinsic_instr_create(b->shader, intrin->intrinsic); 43 intr->const_index[0] = intrin->const_index[0]; 44 intr->const_index[1] = intrin->const_index[1]; 46 if (nir_intrinsic_infos[intrin->intrinsic].num_srcs == 2) 47 nir_src_copy(&intr->src[1], &intrin->src[1], intr); 55 lower_subgroup_op_to_32bit(nir_builder b, nir_intrinsic_instr intrin) argument 57 assert(intrin 115 lower_subgroup_op_to_scalar(nir_builder b,nir_intrinsic_instr * intrin,bool lower_to_32bit) argument 155 lower_vote_eq_to_scalar(nir_builder * b,nir_intrinsic_instr * intrin) argument 181 lower_vote_eq_to_ballot(nir_builder * b,nir_intrinsic_instr * intrin,const nir_lower_subgroups_options * options) argument 226 lower_shuffle(nir_builder * b,nir_intrinsic_instr * intrin,bool lower_to_scalar,bool lower_to_32bit) argument 290 lower_subgroups_intrin(nir_builder * b,nir_intrinsic_instr * intrin,const nir_lower_subgroups_options * options) argument 495 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:lower_subgroups_impl [all...]
H A D	nir_lower_array_deref_of_vec.c	76 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_array_deref_of_vec_impl 77 assert(intrin->intrinsic != nir_intrinsic_copy_deref); 79 if (intrin->intrinsic != nir_intrinsic_load_deref && 80 intrin->intrinsic != nir_intrinsic_interp_deref_at_centroid && 81 intrin->intrinsic != nir_intrinsic_interp_deref_at_sample && 82 intrin->intrinsic != nir_intrinsic_interp_deref_at_offset && 83 intrin->intrinsic != nir_intrinsic_store_deref) 86 nir_deref_instr deref = nir_src_as_deref(intrin->src[0]); 98 assert(intrin->num_components == 1); 102 b.cursor = nir_after_instr(&intrin [all...]
H A D	nir_lower_non_uniform_access.c	97 lower_non_uniform_access_intrin(nir_builder b, nir_intrinsic_instr intrin, argument 100 if (!(nir_intrinsic_access(intrin) & ACCESS_NON_UNIFORM)) 104 if (nir_src_is_const(intrin->src[handle_src])) 107 b->cursor = nir_instr_remove(&intrin->instr); 111 assert(intrin->src[handle_src].is_ssa); 112 assert(intrin->src[handle_src].ssa->num_components == 1); 113 nir_ssa_def handle = intrin->src[handle_src].ssa; 117 nir_builder_instr_insert(b, &intrin->instr); 144 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:nir_lower_non_uniform_access_impl 145 switch (intrin [all...]
/xsrc/external/mit/MesaLib.old/dist/src/intel/vulkan/
H A D	anv_nir_lower_push_constants.c	`38 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:anv_nir_lower_push_constants 41 if (intrin->intrinsic != nir_intrinsic_load_push_constant) 45 intrin->intrinsic = nir_intrinsic_load_uniform;`
H A D	anv_nir_apply_pipeline_layout.c	107 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:get_used_bindings_block 108 switch (intrin->intrinsic) { 110 add_binding(state, nir_intrinsic_desc_set(intrin), 111 nir_intrinsic_binding(intrin)); 129 add_deref_src_binding(state, intrin->src[0]); 157 nir_intrinsic_instr intrin = nir_src_as_intrinsic(src); local in function:find_descriptor_for_index_src 159 while (intrin && intrin->intrinsic == nir_intrinsic_vulkan_resource_reindex) 160 intrin = nir_src_as_intrinsic(intrin 189 nir_intrinsic_instr intrin = nir_src_as_intrinsic(deref->parent); local in function:nir_deref_find_descriptor 197 build_index_for_res_reindex(nir_intrinsic_instr intrin,struct apply_pipeline_layout_state * state) argument 257 try_lower_direct_buffer_intrinsic(nir_intrinsic_instr * intrin,bool is_atomic,struct apply_pipeline_layout_state * state) argument 298 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_direct_buffer_access 352 lower_res_index_intrinsic(nir_intrinsic_instr intrin,struct apply_pipeline_layout_state * state) argument 437 lower_res_reindex_intrinsic(nir_intrinsic_instr * intrin,struct apply_pipeline_layout_state * state) argument 543 lower_load_vulkan_descriptor(nir_intrinsic_instr * intrin,struct apply_pipeline_layout_state * state) argument 645 lower_get_buffer_size(nir_intrinsic_instr * intrin,struct apply_pipeline_layout_state * state) argument 722 lower_image_intrinsic(nir_intrinsic_instr * intrin,struct apply_pipeline_layout_state * state) argument 776 lower_load_constant(nir_intrinsic_instr * intrin,struct apply_pipeline_layout_state * state) argument 1029 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:apply_pipeline_layout_block [all...]
/xsrc/external/mit/MesaLib/src/compiler/nir/
H A D	nir_builder_opcodes.h	4237 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_accept_ray_intersection 4241 nir_builder_instr_insert(build, &intrin->instr); 4242 return intrin; 4247 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_addr_mode_is 4250 nir_ssa_dest_init(&intrin->instr, &intrin->dest, 1, bit_size, NULL); 4251 intrin->src[0] = nir_src_for_ssa(src0); 4252 nir_intrinsic_set_memory_modes(intrin, indices.memory_modes); 4254 nir_builder_instr_insert(build, &intrin->instr); 4255 return &intrin 4260 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_alloc_vertices_and_primitives_amd 4272 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_add 4286 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_add_deref 4299 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_and 4313 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_and_deref 4326 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_comp_swap 4341 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_comp_swap_deref 4355 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_exchange 4369 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_exchange_deref 4382 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_inc 4395 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_inc_deref 4407 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_max 4421 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_max_deref 4434 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_min 4448 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_min_deref 4461 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_or 4475 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_or_deref 4488 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_post_dec 4501 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_post_dec_deref 4513 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_pre_dec 4526 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_pre_dec_deref 4538 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_read 4551 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_read_deref 4563 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_xor 4577 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_atomic_counter_xor_deref 4590 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot 4603 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot_bit_count_exclusive 4615 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot_bit_count_inclusive 4627 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot_bit_count_reduce 4639 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot_bitfield_extract 4652 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot_find_lsb 4664 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ballot_find_msb 4676 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_begin_invocation_interlock 4686 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_add 4705 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_and 4724 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_comp_swap 4744 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_dec_wrap 4763 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_exchange 4782 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_fadd 4801 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_fmax 4820 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_fmin 4839 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_imax 4858 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_imin 4877 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_inc_wrap 4896 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_or 4915 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_umax 4934 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_umin 4953 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_atomic_xor 4972 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_format 4988 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_load 5009 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_load_raw_intel 5027 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_order 5043 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_samples 5059 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_size 5077 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_sparse_load 5098 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_store 5119 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_image_store_raw_intel 5137 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bindless_resource_ir3 5150 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_btd_retire_intel 5160 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_btd_spawn_intel 5172 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_btd_stack_push_intel 5183 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_bvh64_intersect_ray_amd 5200 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_byte_permute_amd 5214 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_cond_end_ir3 5225 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_control_barrier 5235 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_convert_alu_types 5252 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_copy_deref 5266 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_demote 5276 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_demote_if 5287 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_add 5301 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_and 5315 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_comp_swap 5330 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_exchange 5344 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_fadd 5358 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_fcomp_swap 5373 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_fmax 5387 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_fmin 5401 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_imax 5415 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_imin 5429 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_or 5443 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_umax 5457 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_umin 5471 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_atomic_xor 5485 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_buffer_array_length 5498 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_deref_mode_is 5511 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_discard 5521 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_discard_if 5532 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_elect 5543 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_emit_vertex 5554 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_emit_vertex_with_counter 5567 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_end_invocation_interlock 5577 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_end_patch_ir3 5587 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_end_primitive 5598 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_end_primitive_with_counter 5611 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_exclusive_scan 5625 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_execute_callable 5637 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_export_primitive_amd 5648 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_export_vertex_amd 5658 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_first_invocation 5669 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_gds_atomic_add_amd 5684 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_get_ssbo_size 5697 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_get_ubo_size 5709 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_add 5723 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_and 5737 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_comp_swap 5752 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_exchange 5766 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_fadd 5780 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_fcomp_swap 5795 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_fmax 5809 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_fmin 5823 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_imax 5837 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_imin 5851 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_or 5865 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_umax 5879 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_umin 5893 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_global_atomic_xor 5907 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_group_memory_barrier 5917 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_has_input_primitive_amd 5928 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_has_input_vertex_amd 5939 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ignore_ray_intersection 5949 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_add 5968 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_and 5987 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_comp_swap 6007 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_dec_wrap 6026 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_exchange 6045 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_fadd 6064 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_fmax 6083 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_fmin 6102 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_imax 6121 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_imin 6140 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_inc_wrap 6159 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_or 6178 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_umax 6197 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_umin 6216 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_atomic_xor 6235 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_add 6254 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_and 6273 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_comp_swap 6293 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_dec_wrap 6312 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_exchange 6331 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_fadd 6350 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_fmax 6369 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_fmin 6388 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_imax 6407 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_imin 6426 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_inc_wrap 6445 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_or 6464 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_umax 6483 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_umin 6502 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_atomic_xor 6521 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_format 6537 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_load 6558 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_load_param_intel 6572 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_load_raw_intel 6590 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_order 6606 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_samples 6622 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_size 6640 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_sparse_load 6661 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_store 6682 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_deref_store_raw_intel 6700 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_format 6716 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_load 6737 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_load_raw_intel 6755 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_order 6771 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_samples 6787 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_size 6805 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_sparse_load 6826 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_store 6847 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_image_store_raw_intel 6865 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_inclusive_scan 6879 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_interp_deref_at_centroid 6892 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_interp_deref_at_offset 6906 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_interp_deref_at_sample 6920 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_interp_deref_at_vertex 6934 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_is_helper_invocation 6945 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_is_sparse_texels_resident 6957 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_lane_permute_16_amd 6971 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_last_invocation 6982 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_aa_line_width 6993 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_back_face_agx 7004 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_barycentric_at_offset 7017 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_barycentric_at_sample 7030 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_barycentric_centroid 7042 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_barycentric_model 7054 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_barycentric_pixel 7066 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_barycentric_sample 7078 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_base_global_invocation_id 7089 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_base_instance 7100 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_base_vertex 7111 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_base_workgroup_id 7122 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_a_float 7133 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_aaaa8888_unorm 7144 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_b_float 7155 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_g_float 7166 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_r_float 7177 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_rgba 7188 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_blend_const_color_rgba8888_unorm 7199 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_btd_dss_id_intel 7210 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_btd_global_arg_addr_intel 7221 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_btd_local_arg_addr_intel 7232 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_btd_resume_sbt_addr_intel 7243 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_btd_stack_id_intel 7254 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_buffer_amd 7273 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_callable_sbt_addr_intel 7284 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_callable_sbt_stride_intel 7295 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_color0 7306 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_color1 7317 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_constant 7334 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_constant_base_ptr 7346 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_cull_any_enabled_amd 7357 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_cull_back_face_enabled_amd 7368 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_cull_ccw_amd 7379 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_cull_front_face_enabled_amd 7390 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_cull_small_prim_precision_amd 7401 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_cull_small_primitives_enabled_amd 7412 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_deref 7426 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_deref_block_intel 7440 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_desc_set_address_intel 7452 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_draw_id 7463 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_fb_layers_v3d 7474 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_first_vertex 7485 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_frag_coord 7496 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_frag_shading_rate 7507 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_front_face 7518 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_fs_input_interp_deltas 7533 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global 7549 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_block_intel 7565 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_const_block_intel 7580 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_constant 7596 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_constant_bounded 7614 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_constant_offset 7631 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_invocation_id 7642 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_invocation_id_zero_base 7653 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_invocation_index 7664 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_global_ir3 7681 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_gs_header_ir3 7692 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_gs_vertex_offset_amd 7704 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_helper_invocation 7715 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_hs_patch_stride_ir3 7726 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_initial_edgeflags_amd 7737 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_input 7754 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_input_vertex 7772 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_instance_id 7783 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_interpolated_input 7801 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_intersection_opaque_amd 7812 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_invocation_id 7823 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_is_indexed_draw 7834 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_kernel_input 7851 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_layer_id 7862 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_leaf_opaque_intel 7873 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_leaf_procedural_intel 7884 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_line_coord 7895 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_line_width 7906 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_local_invocation_id 7917 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_local_invocation_index 7928 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_local_shared_r600 7941 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_num_subgroups 7952 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_num_workgroups 7963 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_output 7980 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_packed_passthrough_primitive_amd 7991 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_param 8004 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_patch_vertices_in 8015 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_per_primitive_output 8033 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_per_vertex_input 8051 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_per_vertex_output 8069 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_point_coord 8080 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_primitive_id 8091 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_primitive_location_ir3 8103 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_printf_buffer_address 8114 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ptr_dxil 8128 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_push_constant 8143 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_raw_output_pan 8157 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_base_mem_addr_intel 8168 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_flags 8179 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_geometry_index 8190 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_hit_kind 8201 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_hit_sbt_addr_intel 8212 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_hit_sbt_stride_intel 8223 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_hw_stack_size_intel 8234 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_instance_custom_index 8245 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_launch_id 8256 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_launch_size 8267 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_miss_sbt_addr_intel 8278 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_miss_sbt_stride_intel 8289 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_num_dss_rt_stacks_intel 8300 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_object_direction 8311 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_object_origin 8322 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_object_to_world 8334 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_sw_stack_size_intel 8345 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_t_max 8356 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_t_min 8367 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_world_direction 8378 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_world_origin 8389 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ray_world_to_object 8401 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_rel_patch_id_ir3 8412 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_reloc_const_intel 8424 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ring_es2gs_offset_amd 8435 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ring_esgs_amd 8446 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ring_tess_factors_amd 8457 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ring_tess_factors_offset_amd 8468 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ring_tess_offchip_amd 8479 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ring_tess_offchip_offset_amd 8490 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_rt_arg_scratch_offset_amd 8501 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sample_id 8512 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sample_id_no_per_sample 8523 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sample_mask_in 8534 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sample_pos 8545 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sample_pos_from_id 8557 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sample_positions_pan 8568 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sampler_lod_parameters_pan 8581 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_sbt_amd 8593 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_scratch 8608 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_scratch_base_ptr 8621 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_scratch_dxil 8634 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shader_query_enabled_amd 8645 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shader_record_ptr 8656 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shared 8672 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shared_base_ptr 8684 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shared_block_intel 8700 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shared_dxil 8713 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_shared_ir3 8729 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_simd_width_intel 8740 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_size_ir3 8751 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ssbo 8768 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ssbo_address 8781 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ssbo_block_intel 8798 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ssbo_ir3 8816 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_eq_mask 8828 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_ge_mask 8840 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_gt_mask 8852 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_id 8863 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_id_shift_ir3 8874 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_invocation 8885 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_le_mask 8897 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_lt_mask 8909 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_subgroup_size 8920 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tcs_header_ir3 8931 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tcs_in_param_base_r600 8942 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tcs_num_patches_amd 8953 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tcs_out_param_base_r600 8964 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tcs_rel_patch_id_r600 8975 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tcs_tess_factor_base_r600 8986 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_coord 8997 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_coord_r600 9008 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_factor_base_ir3 9019 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_level_inner 9030 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_level_inner_default 9041 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_level_outer 9052 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_level_outer_default 9063 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_param_base_ir3 9074 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tess_rel_patch_id_amd 9085 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_texture_rect_scaling 9097 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_tlb_color_v3d 9112 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ubo 9131 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ubo_dxil 9145 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_ubo_vec4 9161 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_uniform 9177 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_user_clip_plane 9189 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_user_data_amd 9200 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_vertex_id 9211 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_vertex_id_zero_base 9222 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_view_index 9233 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_offset 9244 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_scale 9255 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_x_offset 9266 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_x_scale 9277 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_y_offset 9288 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_y_scale 9299 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_z_offset 9310 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_viewport_z_scale 9321 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_vs_primitive_stride_ir3 9332 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_vs_vertex_stride_ir3 9343 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_vulkan_descriptor 9357 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_work_dim 9368 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_workgroup_id 9379 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_workgroup_id_zero_base 9390 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_workgroup_num_input_primitives_amd 9401 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_workgroup_num_input_vertices_amd 9412 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_load_workgroup_size 9423 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_masked_swizzle_amd 9437 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_mbcnt_amd 9450 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memcpy_deref 9465 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memory_barrier 9475 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memory_barrier_atomic_counter 9485 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memory_barrier_buffer 9495 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memory_barrier_image 9505 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memory_barrier_shared 9515 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_memory_barrier_tcs_patch 9525 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_nop 9535 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_overwrite_tes_arguments_amd 9549 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_overwrite_vs_arguments_amd 9561 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_printf 9574 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_quad_broadcast 9588 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_quad_swap_diagonal 9601 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_quad_swap_horizontal 9614 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_quad_swap_vertical 9627 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_quad_swizzle_amd 9641 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_read_first_invocation 9654 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_read_invocation 9668 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_read_invocation_cond_ir3 9682 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_reduce 9697 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_report_ray_intersection 9710 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_rt_execute_callable 9724 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_rt_resume 9736 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_rt_return_amd 9746 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_rt_trace_ray 9769 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_scoped_barrier 9783 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_set_vertex_and_primitive_count 9796 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shader_clock 9808 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_add 9822 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_add_dxil 9835 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_and 9849 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_and_dxil 9862 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_comp_swap 9877 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_comp_swap_dxil 9891 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_exchange 9905 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_exchange_dxil 9918 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_fadd 9932 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_fcomp_swap 9947 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_fmax 9961 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_fmin 9975 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_imax 9989 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_imax_dxil 10002 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_imin 10016 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_imin_dxil 10029 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_or 10043 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_or_dxil 10056 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_umax 10070 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_umax_dxil 10083 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_umin 10097 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_umin_dxil 10110 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_xor 10124 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shared_atomic_xor_dxil 10137 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shuffle 10151 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shuffle_down 10165 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shuffle_up 10179 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_shuffle_xor 10193 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_sparse_residency_code_and 10206 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_add 10221 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_add_ir3 10237 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_and 10252 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_and_ir3 10268 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_comp_swap 10284 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_comp_swap_ir3 10301 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_exchange 10316 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_exchange_ir3 10332 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_fadd 10347 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_fcomp_swap 10363 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_fmax 10378 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_fmin 10393 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_imax 10408 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_imax_ir3 10424 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_imin 10439 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_imin_ir3 10455 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_or 10470 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_or_ir3 10486 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_umax 10501 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_umax_ir3 10517 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_umin 10532 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_umin_ir3 10548 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_xor 10563 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_ssbo_atomic_xor_ir3 10579 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_buffer_amd 10599 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_combined_output_pan 10617 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_deref 10632 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_deref_block_intel 10647 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_global 10664 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_global_block_intel 10681 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_global_ir3 10698 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_local_shared_r600 10712 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_output 10730 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_per_primitive_output 10749 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_per_vertex_output 10768 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_raw_output_pan 10780 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_scratch 10796 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_scratch_dxil 10808 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_shared 10825 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_shared_block_intel 10842 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_shared_dxil 10854 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_shared_ir3 10870 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_shared_masked_dxil 10883 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_ssbo 10901 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_ssbo_block_intel 10919 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_ssbo_ir3 10938 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_ssbo_masked_dxil 10952 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_tf_r600 10964 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_store_tlb_sample_color_v3d 10980 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_terminate 10990 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_terminate_if 11001 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_terminate_ray 11011 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_trace_ray 11032 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_trace_ray_commit_intel 11042 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_trace_ray_continue_intel 11052 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_trace_ray_initial_intel 11062 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_vote_all 11074 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_vote_any 11086 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_vote_feq 11099 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_vote_ieq 11112 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_vulkan_resource_index 11128 nir_intrinsic_instr intrin = nir_intrinsic_instr_create( local in function:_nir_build_vulkan_resource_reindex 11143 nir_intrinsic_instr *intrin = nir_intrinsic_instr_create( local in function:_nir_build_write_invocation_amd [all...]
/xsrc/external/mit/MesaLib/dist/src/intel/compiler/
H A D	brw_nir_lower_mem_access_bit_sizes.c	30 dup_mem_intrinsic(nir_builder b, nir_intrinsic_instr intrin, argument 35 const nir_intrinsic_info info = &nir_intrinsic_infos[intrin->intrinsic]; 38 nir_intrinsic_instr_create(b->shader, intrin->intrinsic); 40 nir_src intrin_offset_src = nir_get_io_offset_src(intrin); 42 assert(intrin->src[i].is_ssa); 45 assert(&intrin->src[i] != intrin_offset_src); 47 } else if (&intrin->src[i] == intrin_offset_src) { 48 dup->src[i] = nir_src_for_ssa(nir_iadd_imm(b, intrin->src[i].ssa, 51 dup->src[i] = nir_src_for_ssa(intrin->src[i].ssa); 56 if (intrin 82 lower_mem_load_bit_size(nir_builder * b,nir_intrinsic_instr * intrin,const struct intel_device_info * devinfo) argument 156 lower_mem_store_bit_size(nir_builder * b,nir_intrinsic_instr * intrin,const struct intel_device_info * devinfo) argument 254 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:lower_mem_access_bit_sizes_instr [all...]
/xsrc/external/mit/MesaLib.old/dist/src/intel/compiler/
H A D	brw_nir_lower_mem_access_bit_sizes.c	30 dup_mem_intrinsic(nir_builder b, nir_intrinsic_instr intrin, argument 35 const nir_intrinsic_info info = &nir_intrinsic_infos[intrin->intrinsic]; 38 nir_intrinsic_instr_create(b->shader, intrin->intrinsic); 40 nir_src intrin_offset_src = nir_get_io_offset_src(intrin); 42 assert(intrin->src[i].is_ssa); 45 assert(&intrin->src[i] != intrin_offset_src); 47 } else if (&intrin->src[i] == intrin_offset_src) { 48 dup->src[i] = nir_src_for_ssa(nir_iadd_imm(b, intrin->src[i].ssa, 51 dup->src[i] = nir_src_for_ssa(intrin->src[i].ssa); 58 dup->const_index[i] = intrin 77 lower_mem_load_bit_size(nir_builder * b,nir_intrinsic_instr * intrin) argument 157 lower_mem_store_bit_size(nir_builder * b,nir_intrinsic_instr * intrin) argument 258 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(instr); local in function:lower_mem_access_bit_sizes_impl [all...]
/xsrc/external/mit/MesaLib.old/dist/src/compiler/spirv/
H A D	vtn_subgroup.c	52 nir_intrinsic_instr intrin = local in function:vtn_build_subgroup_instr 54 nir_ssa_dest_init_for_type(&intrin->instr, &intrin->dest, 56 intrin->num_components = intrin->dest.ssa.num_components; 58 intrin->src[0] = nir_src_for_ssa(src0->def); 60 intrin->src[1] = nir_src_for_ssa(index); 62 intrin->const_index[0] = const_idx0; 63 intrin->const_index[1] = const_idx1; 65 nir_builder_instr_insert(&b->nb, &intrin 109 nir_intrinsic_instr intrin = local in function:vtn_handle_subgroup 164 nir_intrinsic_instr intrin = local in function:vtn_handle_subgroup 227 nir_intrinsic_instr intrin = local in function:vtn_handle_subgroup [all...]
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/lima/ir/
H A D	lima_nir_split_load_input.c	51 nir_intrinsic_instr *intrin = nir_instr_as_intrinsic(ssa->parent_instr); local in function:lima_nir_split_load_input_instr 52 if (intrin->intrinsic != nir_intrinsic_load_input) 74 b->cursor = nir_before_instr(&intrin->instr); 77 intrin->intrinsic); 83 nir_intrinsic_set_base(new_intrin, nir_intrinsic_base(intrin)); 84 nir_intrinsic_set_component(new_intrin, nir_intrinsic_component(intrin) + swizzle); 85 nir_intrinsic_set_dest_type(new_intrin, nir_intrinsic_dest_type(intrin)); 88 nir_src_copy(&new_intrin->src[0], &intrin->src[0]);
/xsrc/external/mit/MesaLib/dist/src/gallium/drivers/r600/sfn/
H A D	sfn_emitssboinstruction.h	`31 bool emit_image_size(const nir_intrinsic_instr intrin); 32 bool emit_image_load(const nir_intrinsic_instr intrin); 33 bool emit_image_store(const nir_intrinsic_instr intrin); 34 bool emit_ssbo_atomic_op(const nir_intrinsic_instr intrin); 35 bool emit_buffer_size(const nir_intrinsic_instr intrin); 37 bool fetch_return_value(const nir_intrinsic_instr intrin);`
/xsrc/external/mit/MesaLib/dist/src/compiler/spirv/
H A D	vtn_amd.c	82 nir_intrinsic_instr intrin = nir_intrinsic_instr_create(b->nb.shader, op); local in function:vtn_handle_amd_shader_ballot_instruction 83 nir_ssa_dest_init_for_type(&intrin->instr, &intrin->dest, dest_type, NULL); 85 intrin->num_components = intrin->dest.ssa.num_components; 88 intrin->src[i] = nir_src_for_ssa(vtn_get_nir_ssa(b, w[i + 5])); 90 if (intrin->intrinsic == nir_intrinsic_quad_swizzle_amd) { 96 nir_intrinsic_set_swizzle_mask(intrin, mask); 98 } else if (intrin->intrinsic == nir_intrinsic_masked_swizzle_amd) { 103 nir_intrinsic_set_swizzle_mask(intrin, mas 192 nir_intrinsic_instr intrin = nir_intrinsic_instr_create(b->nb.shader, op); local in function:vtn_handle_amd_shader_explicit_vertex_parameter_instruction [all...]
/xsrc/external/mit/MesaLib/dist/src/amd/common/
H A D	ac_nir_lower_tess_io_to_mem.c	158 nir_intrinsic_instr intrin, 162 bool indirect = !nir_src_is_const(nir_get_io_offset_src(intrin)); 166 uint64_t slot = nir_intrinsic_io_semantics(intrin).location; 168 intrin->intrinsic != nir_intrinsic_load_per_vertex_input && 169 intrin->intrinsic != nir_intrinsic_store_per_vertex_output) 176 tcs_output_needs_vmem(nir_intrinsic_instr intrin, argument 179 uint64_t mask = intrin->intrinsic == nir_intrinsic_store_per_vertex_output 183 return match_mask(MESA_SHADER_TESS_CTRL, intrin, mask, true); 187 tcs_output_needs_lds(nir_intrinsic_instr intrin, argument 190 uint64_t mask = intrin 157 match_mask(gl_shader_stage stage,nir_intrinsic_instr * intrin,uint64_t mask,bool match_indirect) argument 205 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_ls_output_store 245 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:filter_load_tcs_per_vertex_input 287 hs_output_lds_offset(nir_builder * b,lower_tess_io_state * st,nir_intrinsic_instr * intrin) argument 325 hs_per_vertex_output_vmem_offset(nir_builder * b,lower_tess_io_state * st,nir_intrinsic_instr * intrin) argument 347 hs_per_patch_output_vmem_offset(nir_builder * b,lower_tess_io_state * st,nir_intrinsic_instr * intrin,unsigned const_base_offset) argument 379 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_hs_per_vertex_input_load 387 lower_hs_output_store(nir_builder b,nir_intrinsic_instr * intrin,lower_tess_io_state * st) argument 426 lower_hs_output_load(nir_builder * b,nir_intrinsic_instr * intrin,lower_tess_io_state * st) argument 436 update_hs_scoped_barrier(nir_intrinsic_instr * intrin) argument 453 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_hs_output_access 582 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_tes_input_load 600 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:filter_hs_output_access 615 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:filter_any_input_access 723 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:filter_const_lowerable_tess_intrinsics 734 nir_intrinsic_instr intrin = nir_instr_as_intrinsic(instr); local in function:lower_tess_intrinsics_to_const [all...]

Completed in 48 milliseconds

12 3 4 5 6 7 8 9