| /third_party/mesa3d/src/gallium/drivers/radeonsi/ |
| D | si_shader_nir.c | 57 void si_nir_opts(struct si_screen *sscreen, struct nir_shader *nir, bool first) in si_nir_opts() argument
66 NIR_PASS(progress, nir, nir_lower_vars_to_ssa); in si_nir_opts()
67 NIR_PASS(progress, nir, nir_lower_alu_to_scalar, si_alu_to_scalar_filter, sscreen); in si_nir_opts()
68 NIR_PASS(progress, nir, nir_lower_phis_to_scalar, false); in si_nir_opts()
71 NIR_PASS(progress, nir, nir_split_array_vars, nir_var_function_temp); in si_nir_opts()
72 NIR_PASS(lower_alu_to_scalar, nir, nir_shrink_vec_array_vars, nir_var_function_temp); in si_nir_opts()
73 NIR_PASS(progress, nir, nir_opt_find_array_copies); in si_nir_opts()
75 NIR_PASS(progress, nir, nir_opt_copy_prop_vars); in si_nir_opts()
76 NIR_PASS(progress, nir, nir_opt_dead_write_vars); in si_nir_opts()
78 NIR_PASS(lower_alu_to_scalar, nir, nir_opt_trivial_continues); in si_nir_opts()
[all …]
|
| D | si_shader_info.c | 173 static bool are_tessfactors_def_in_all_invocs(const struct nir_shader *nir) in are_tessfactors_def_in_all_invocs() argument
175 assert(nir->info.stage == MESA_SHADER_TESS_CTRL); in are_tessfactors_def_in_all_invocs()
193 nir_foreach_function (function, nir) { in are_tessfactors_def_in_all_invocs()
222 static void scan_io_usage(const nir_shader *nir, struct si_shader_info *info, in scan_io_usage() argument
275 if (nir->info.stage != MESA_SHADER_VERTEX || !is_input) in scan_io_usage()
278 if (nir->info.stage == MESA_SHADER_FRAGMENT && !is_input) { in scan_io_usage()
360 if (nir->info.stage == MESA_SHADER_FRAGMENT && in scan_io_usage()
391 static void scan_instruction(const struct nir_shader *nir, struct si_shader_info *info, in scan_instruction() argument
442 if (nir->info.stage == MESA_SHADER_VERTEX || in scan_instruction()
443 nir->info.stage == MESA_SHADER_TESS_EVAL) in scan_instruction()
[all …]
|
| /third_party/mesa3d/src/compiler/nir/ |
| D | nir_sweep.c | 41 static void sweep_cf_node(nir_shader *nir, nir_cf_node *cf_node);
44 sweep_block(nir_shader *nir, nir_block *block) in sweep_block() argument
46 ralloc_steal(nir, block); in sweep_block()
59 list_add(&instr->gc_node, &nir->gc_list); in sweep_block()
64 sweep_if(nir_shader *nir, nir_if *iff) in sweep_if() argument
66 ralloc_steal(nir, iff); in sweep_if()
69 sweep_cf_node(nir, cf_node); in sweep_if()
73 sweep_cf_node(nir, cf_node); in sweep_if()
78 sweep_loop(nir_shader *nir, nir_loop *loop) in sweep_loop() argument
80 ralloc_steal(nir, loop); in sweep_loop()
[all …]
|
| D | nir_lower_clip_cull_distance_arrays.c | 41 get_unwrapped_array_length(nir_shader *nir, nir_variable *var) in get_unwrapped_array_length() argument
51 if (nir_is_arrayed_io(var, nir->info.stage)) in get_unwrapped_array_length()
65 combine_clip_cull(nir_shader *nir, in combine_clip_cull() argument
72 nir_foreach_variable_with_modes(var, nir, mode) { in combine_clip_cull()
86 nir->info.clip_distance_array_size = 0; in combine_clip_cull()
87 nir->info.cull_distance_array_size = 0; in combine_clip_cull()
104 const unsigned clip_array_size = get_unwrapped_array_length(nir, clip); in combine_clip_cull()
105 const unsigned cull_array_size = get_unwrapped_array_length(nir, cull); in combine_clip_cull()
108 nir->info.clip_distance_array_size = clip_array_size; in combine_clip_cull()
109 nir->info.cull_distance_array_size = cull_array_size; in combine_clip_cull()
[all …]
|
| /third_party/mesa3d/src/imagination/rogue/ |
| D | rogue_nir.c | 78 nir_shader *nir, in rogue_nir_passes() argument
83 nir_validate_shader(nir, "after spirv_to_nir"); in rogue_nir_passes()
86 NIR_PASS_V(nir, nir_split_var_copies); in rogue_nir_passes()
87 NIR_PASS_V(nir, nir_split_per_member_structs); in rogue_nir_passes()
90 NIR_PASS_V(nir, nir_lower_clamp_color_outputs); in rogue_nir_passes()
93 NIR_PASS_V(nir, in rogue_nir_passes()
100 NIR_PASS_V(nir, nir_lower_io_to_scalar, nir_var_shader_in); in rogue_nir_passes()
107 NIR_PASS_V(nir, nir_opt_access, &opt_access_options); in rogue_nir_passes()
110 if (nir->info.stage == MESA_SHADER_FRAGMENT) in rogue_nir_passes()
111 NIR_PASS_V(nir, rogue_nir_pfo); in rogue_nir_passes()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/lima/standalone/ |
| D | lima_compiler_cmdline.c | 62 sort_varyings(nir_shader *nir, nir_variable_mode mode) in sort_varyings() argument
66 nir_foreach_variable_with_modes_safe(var, nir, mode) { in sort_varyings()
70 exec_list_append(&nir->variables, &new_list); in sort_varyings()
74 fixup_varying_slots(nir_shader *nir, nir_variable_mode mode) in fixup_varying_slots() argument
76 nir_foreach_variable_with_modes(var, nir, mode) { in fixup_varying_slots()
115 nir_shader *nir = glsl_to_nir(&local_ctx.Const, prog, stage, nir_options); in load_glsl() local
119 nir->info.stage == MESA_SHADER_VERTEX || in load_glsl()
120 nir->info.stage == MESA_SHADER_GEOMETRY) { in load_glsl()
121 NIR_PASS_V(nir, nir_lower_io_to_temporaries, in load_glsl()
122 nir_shader_get_entrypoint(nir), in load_glsl()
[all …]
|
| /third_party/mesa3d/src/mesa/state_tracker/ |
| D | st_glsl_to_nir.cpp | 94 st_nir_assign_vs_in_locations(struct nir_shader *nir) in st_nir_assign_vs_in_locations() argument
96 if (nir->info.stage != MESA_SHADER_VERTEX || nir->info.io_lowered) in st_nir_assign_vs_in_locations()
99 nir->num_inputs = util_bitcount64(nir->info.inputs_read); in st_nir_assign_vs_in_locations()
103 nir_foreach_shader_in_variable_safe(var, nir) { in st_nir_assign_vs_in_locations()
107 if (nir->info.inputs_read & BITFIELD64_BIT(var->data.location)) { in st_nir_assign_vs_in_locations()
109 util_bitcount64(nir->info.inputs_read & in st_nir_assign_vs_in_locations()
124 NIR_PASS_V(nir, nir_lower_global_vars_to_local); in st_nir_assign_vs_in_locations()
180 nir_shader *nir) in st_nir_assign_uniform_locations() argument
185 nir_foreach_variable_with_modes(uniform, nir, nir_var_uniform | in st_nir_assign_uniform_locations()
236 st_nir_add_point_size(nir_shader *nir) in st_nir_add_point_size() argument
[all …]
|
| D | st_program.c | 354 st_finalize_nir_before_variants(struct nir_shader *nir) in st_finalize_nir_before_variants() argument
356 NIR_PASS_V(nir, nir_split_var_copies); in st_finalize_nir_before_variants()
357 NIR_PASS_V(nir, nir_lower_var_copies); in st_finalize_nir_before_variants()
358 if (nir->options->lower_all_io_to_temps || in st_finalize_nir_before_variants()
359 nir->options->lower_all_io_to_elements || in st_finalize_nir_before_variants()
360 nir->info.stage == MESA_SHADER_VERTEX || in st_finalize_nir_before_variants()
361 nir->info.stage == MESA_SHADER_GEOMETRY) { in st_finalize_nir_before_variants()
362 NIR_PASS_V(nir, nir_lower_io_arrays_to_elements_no_indirects, false); in st_finalize_nir_before_variants()
363 } else if (nir->info.stage == MESA_SHADER_FRAGMENT) { in st_finalize_nir_before_variants()
364 NIR_PASS_V(nir, nir_lower_io_arrays_to_elements_no_indirects, true); in st_finalize_nir_before_variants()
[all …]
|
| D | st_nir_builtins.c | 34 nir_shader *nir) in st_nir_finish_builtin_shader() argument
37 gl_shader_stage stage = nir->info.stage; in st_nir_finish_builtin_shader()
39 nir->info.separate_shader = true; in st_nir_finish_builtin_shader()
41 nir->info.fs.untyped_color_outputs = true; in st_nir_finish_builtin_shader()
43 NIR_PASS_V(nir, nir_lower_global_vars_to_local); in st_nir_finish_builtin_shader()
44 NIR_PASS_V(nir, nir_split_var_copies); in st_nir_finish_builtin_shader()
45 NIR_PASS_V(nir, nir_lower_var_copies); in st_nir_finish_builtin_shader()
46 NIR_PASS_V(nir, nir_lower_system_values); in st_nir_finish_builtin_shader()
47 NIR_PASS_V(nir, nir_lower_compute_system_values, NULL); in st_nir_finish_builtin_shader()
49 if (nir->options->lower_to_scalar) { in st_nir_finish_builtin_shader()
[all …]
|
| /third_party/mesa3d/src/gallium/drivers/freedreno/ir3/ |
| D | ir3_cmdline.c | 81 sort_varyings(nir_shader *nir, nir_variable_mode mode) in sort_varyings() argument
85 nir_foreach_variable_with_modes_safe (var, nir, mode) { in sort_varyings()
89 exec_list_append(&nir->variables, &new_list); in sort_varyings()
93 fixup_varying_slots(nir_shader *nir, nir_variable_mode mode) in fixup_varying_slots() argument
95 nir_foreach_variable_with_modes (var, nir, mode) { in fixup_varying_slots()
124 nir_shader *nir = glsl_to_nir(&local_ctx.Const, prog, stage, nir_options); in load_glsl() local
128 nir->info.stage == MESA_SHADER_VERTEX || in load_glsl()
129 nir->info.stage == MESA_SHADER_GEOMETRY) { in load_glsl()
130 NIR_PASS_V(nir, nir_lower_io_to_temporaries, in load_glsl()
131 nir_shader_get_entrypoint(nir), true, true); in load_glsl()
[all …]
|
| /third_party/mesa3d/src/amd/vulkan/ |
| D | radv_shader_info.c | 37 gather_intrinsic_load_input_info(const nir_shader *nir, const nir_intrinsic_instr *instr, in gather_intrinsic_load_input_info() argument
40 switch (nir->info.stage) { in gather_intrinsic_load_input_info()
55 gather_intrinsic_store_output_info(const nir_shader *nir, const nir_intrinsic_instr *instr, in gather_intrinsic_store_output_info() argument
67 switch (nir->info.stage) { in gather_intrinsic_store_output_info()
89 gather_push_constant_info(const nir_shader *nir, const nir_intrinsic_instr *instr, in gather_push_constant_info() argument
108 gather_intrinsic_info(const nir_shader *nir, const nir_intrinsic_instr *instr, in gather_intrinsic_info() argument
167 gather_push_constant_info(nir, instr, info); in gather_intrinsic_info()
195 gather_intrinsic_load_input_info(nir, instr, info); in gather_intrinsic_info()
198 gather_intrinsic_store_output_info(nir, instr, info); in gather_intrinsic_info()
212 gather_tex_info(const nir_shader *nir, const nir_tex_instr *instr, struct radv_shader_info *info) in gather_tex_info() argument
[all …]
|
| /third_party/mesa3d/src/intel/compiler/ |
| D | brw_kernel.c | 40 nir_shader *nir = nir_load_libclc_shader(64, disk_cache, in load_clc_shader() local
42 if (nir == NULL) in load_clc_shader()
46 p_atomic_cmpxchg(&compiler->clc_shader, NULL, nir); in load_clc_shader()
49 return nir; in load_clc_shader()
52 ralloc_free(nir); in load_clc_shader()
128 implement_intel_builtins(nir_shader *nir) in implement_intel_builtins() argument
132 nir_foreach_function(func, nir) { in implement_intel_builtins()
159 nir_shader_preserve_all_metadata(nir); in implement_intel_builtins()
165 lower_kernel_intrinsics(nir_shader *nir) in lower_kernel_intrinsics() argument
167 nir_function_impl *impl = nir_shader_get_entrypoint(nir); in lower_kernel_intrinsics()
[all …]
|
| D | brw_nir.h | 93 void brw_nir_analyze_boolean_resolves(nir_shader *nir);
96 nir_shader *nir,
103 bool brw_nir_lower_cs_intrinsics(nir_shader *nir);
105 void brw_nir_lower_vs_inputs(nir_shader *nir,
108 void brw_nir_lower_vue_inputs(nir_shader *nir,
110 void brw_nir_lower_tes_inputs(nir_shader *nir, const struct brw_vue_map *vue);
111 void brw_nir_lower_fs_inputs(nir_shader *nir,
114 void brw_nir_lower_vue_outputs(nir_shader *nir);
115 void brw_nir_lower_tcs_outputs(nir_shader *nir, const struct brw_vue_map *vue,
117 void brw_nir_lower_fs_outputs(nir_shader *nir);
[all …]
|
| D | brw_nir.c | 163 brw_nir_lower_vs_inputs(nir_shader *nir, in brw_nir_lower_vs_inputs() argument
168 nir_foreach_shader_in_variable(var, nir) in brw_nir_lower_vs_inputs()
175 nir_lower_io(nir, nir_var_shader_in, type_size_vec4, in brw_nir_lower_vs_inputs()
179 nir_opt_constant_folding(nir); in brw_nir_lower_vs_inputs()
181 nir_io_add_const_offset_to_base(nir, nir_var_shader_in); in brw_nir_lower_vs_inputs()
183 brw_nir_apply_attribute_workarounds(nir, vs_attrib_wa_flags); in brw_nir_lower_vs_inputs()
191 BITSET_TEST(nir->info.system_values_read, SYSTEM_VALUE_FIRST_VERTEX) || in brw_nir_lower_vs_inputs()
192 BITSET_TEST(nir->info.system_values_read, SYSTEM_VALUE_BASE_INSTANCE) || in brw_nir_lower_vs_inputs()
193 BITSET_TEST(nir->info.system_values_read, SYSTEM_VALUE_VERTEX_ID_ZERO_BASE) || in brw_nir_lower_vs_inputs()
194 BITSET_TEST(nir->info.system_values_read, SYSTEM_VALUE_INSTANCE_ID); in brw_nir_lower_vs_inputs()
[all …]
|
| D | brw_nir_lower_cs_intrinsics.c | 28 nir_shader *nir; member
40 nir_shader *nir = state->nir; in lower_cs_intrinsics_convert_block() local
71 if (nir->info.stage == MESA_SHADER_TASK || in lower_cs_intrinsics_convert_block()
72 nir->info.stage == MESA_SHADER_MESH) { in lower_cs_intrinsics_convert_block()
92 if (state->nir->info.workgroup_size_variable) { in lower_cs_intrinsics_convert_block()
97 size_x = nir_imm_int(b, nir->info.workgroup_size[0]); in lower_cs_intrinsics_convert_block()
98 size_y = nir_imm_int(b, nir->info.workgroup_size[1]); in lower_cs_intrinsics_convert_block()
120 switch (state->nir->info.cs.derivative_group) { in lower_cs_intrinsics_convert_block()
122 if (nir->info.num_images == 0 && in lower_cs_intrinsics_convert_block()
123 nir->info.num_textures == 0) { in lower_cs_intrinsics_convert_block()
[all …]
|
| /third_party/mesa3d/src/microsoft/spirv_to_dxil/ |
| D | dxil_spirv_nir.c | 48 add_runtime_data_var(nir_shader *nir, unsigned desc_set, unsigned binding) in add_runtime_data_var() argument
51 nir->info.stage == MESA_SHADER_COMPUTE in add_runtime_data_var()
60 nir, nir_var_mem_ubo, in add_runtime_data_var()
161 add_push_constant_var(nir_shader *nir, unsigned size, unsigned desc_set, unsigned binding) in add_push_constant_var() argument
170 nir, nir_var_mem_ubo, in add_push_constant_var()
560 dxil_spirv_nir_link(nir_shader *nir, nir_shader *prev_stage_nir) in dxil_spirv_nir_link() argument
565 NIR_PASS_V(nir, dxil_spirv_nir_kill_undefined_varyings, prev_stage_nir); in dxil_spirv_nir_link()
566 NIR_PASS_V(prev_stage_nir, dxil_spirv_nir_kill_unused_outputs, nir); in dxil_spirv_nir_link()
568 nir->info.inputs_read = in dxil_spirv_nir_link()
569 dxil_reassign_driver_locations(nir, nir_var_shader_in, in dxil_spirv_nir_link()
[all …]
|
| D | spirv_to_dxil.c | 52 spirv_to_dxil_nir_prep(nir_shader *nir) in spirv_to_dxil_nir_prep() argument
58 NIR_PASS_V(nir, nir_lower_variable_initializers, nir_var_function_temp); in spirv_to_dxil_nir_prep()
59 NIR_PASS_V(nir, nir_lower_returns); in spirv_to_dxil_nir_prep()
60 NIR_PASS_V(nir, nir_inline_functions); in spirv_to_dxil_nir_prep()
61 NIR_PASS_V(nir, nir_copy_prop); in spirv_to_dxil_nir_prep()
62 NIR_PASS_V(nir, nir_opt_deref); in spirv_to_dxil_nir_prep()
65 foreach_list_typed_safe(nir_function, func, node, &nir->functions) { in spirv_to_dxil_nir_prep()
69 assert(exec_list_length(&nir->functions) == 1); in spirv_to_dxil_nir_prep()
76 NIR_PASS_V(nir, nir_lower_variable_initializers, ~0); in spirv_to_dxil_nir_prep()
81 NIR_PASS_V(nir, nir_split_var_copies); in spirv_to_dxil_nir_prep()
[all …]
|
| /third_party/mesa3d/src/microsoft/clc/ |
| D | clc_compiler.c | 258 clc_lower_images(nir_shader *nir, struct clc_image_lower_context *context) in clc_lower_images() argument
260 nir_foreach_function(func, nir) { in clc_lower_images()
284 clc_lower_64bit_semantics(nir_shader *nir) in clc_lower_64bit_semantics() argument
286 nir_foreach_function(func, nir) { in clc_lower_64bit_semantics()
326 clc_lower_nonnormalized_samplers(nir_shader *nir, in clc_lower_nonnormalized_samplers() argument
329 nir_foreach_function(func, nir) { in clc_lower_nonnormalized_samplers()
398 add_kernel_inputs_var(struct clc_dxil_object *dxil, nir_shader *nir, in add_kernel_inputs_var() argument
406 nir_foreach_variable_with_modes(var, nir, nir_var_uniform) in add_kernel_inputs_var()
416 nir_variable_create(nir, nir_var_mem_ubo, in add_kernel_inputs_var()
426 struct nir_shader *nir, unsigned *cbv_id) in add_work_properties_var() argument
[all …]
|
| /third_party/mesa3d/src/asahi/compiler/ |
| D | cmdline.c | 60 sort_varyings(nir_shader *nir, nir_variable_mode mode) in sort_varyings() argument
64 nir_foreach_variable_with_modes_safe (var, nir, mode) { in sort_varyings()
68 exec_list_append(&nir->variables, &new_list); in sort_varyings()
72 fixup_varying_slots(nir_shader *nir, nir_variable_mode mode) in fixup_varying_slots() argument
74 nir_foreach_variable_with_modes (var, nir, mode) { in fixup_varying_slots()
88 nir_shader *nir[2]; in compile_shader() local
110 nir[i] = glsl_to_nir(&local_ctx.Const, prog, shader_types[i], &agx_nir_options); in compile_shader()
113 nir_assign_var_locations(nir[i], nir_var_shader_in, &nir[i]->num_inputs, in compile_shader()
115 sort_varyings(nir[i], nir_var_shader_out); in compile_shader()
116 nir_assign_var_locations(nir[i], nir_var_shader_out, &nir[i]->num_outputs, in compile_shader()
[all …]
|
| /third_party/mesa3d/src/gallium/frontends/clover/nir/ |
| D | invocation.cpp | 345 clover_lower_nir(nir_shader *nir, std::vector<binary::argument> &args, in clover_lower_nir() argument
349 if (nir->constant_data_size) { in clover_lower_nir()
352 constant_var = nir_variable_create(nir, nir_var_uniform, type, in clover_lower_nir()
363 return nir_shader_lower_instructions(nir, in clover_lower_nir()
397 struct disk_cache *clover::nir::create_clc_disk_cache(void) in create_clc_disk_cache()
404 if (!disk_cache_get_function_identifier((void *)clover::nir::create_clc_disk_cache, &ctx)) in create_clc_disk_cache()
413 void clover::nir::check_for_libclc(const device &dev) in check_for_libclc()
419 nir_shader *clover::nir::load_libclc_nir(const device &dev, std::string &r_log) in load_libclc_nir()
436 binary clover::nir::spirv_to_nir(const binary &mod, const device &dev, in spirv_to_nir()
440 std::shared_ptr<nir_shader> nir = dev.clc_nir; in spirv_to_nir() local
[all …]
|
| /third_party/mesa3d/src/vulkan/runtime/ |
| D | vk_nir.c | 100 nir_shader *nir = spirv_to_nir(spirv_data, spirv_size_B / 4, in vk_spirv_to_nir() local
106 if (nir == NULL) in vk_spirv_to_nir()
109 assert(nir->info.stage == stage); in vk_spirv_to_nir()
110 nir_validate_shader(nir, "after spirv_to_nir"); in vk_spirv_to_nir()
111 nir_validate_ssa_dominance(nir, "after spirv_to_nir"); in vk_spirv_to_nir()
113 ralloc_steal(mem_ctx, nir); in vk_spirv_to_nir()
119 NIR_PASS_V(nir, nir_lower_variable_initializers, nir_var_function_temp); in vk_spirv_to_nir()
120 NIR_PASS_V(nir, nir_lower_returns); in vk_spirv_to_nir()
121 NIR_PASS_V(nir, nir_inline_functions); in vk_spirv_to_nir()
122 NIR_PASS_V(nir, nir_copy_prop); in vk_spirv_to_nir()
[all …]
|
| /third_party/mesa3d/src/panfrost/bifrost/ |
| D | cmdline.c | 93 sort_varyings(nir_shader *nir, nir_variable_mode mode) in sort_varyings() argument
97 nir_foreach_variable_with_modes_safe (var, nir, mode) { in sort_varyings()
101 exec_list_append(&nir->variables, &new_list); in sort_varyings()
105 fixup_varying_slots(nir_shader *nir, nir_variable_mode mode) in fixup_varying_slots() argument
107 nir_foreach_variable_with_modes (var, nir, mode) { in fixup_varying_slots()
121 nir_shader *nir[MESA_SHADER_COMPUTE + 1]; in compile_shader() local
152 nir[i] = glsl_to_nir(&local_ctx.Const, prog, shader_types[i], &bifrost_nir_options); in compile_shader()
155 nir_assign_var_locations(nir[i], nir_var_shader_in, &nir[i]->num_inputs, in compile_shader()
157 sort_varyings(nir[i], nir_var_shader_out); in compile_shader()
158 nir_assign_var_locations(nir[i], nir_var_shader_out, &nir[i]->num_outputs, in compile_shader()
[all …]
|
| /third_party/mesa3d/src/gallium/frontends/lavapipe/ |
| D | lvp_pipeline.c | 128 set_image_access(struct lvp_pipeline *pipeline, nir_shader *nir, in set_image_access() argument
139 value += get_set_layout(pipeline->layout, s)->stage[nir->info.stage].image_count; in set_image_access()
141 value += binding->stage[nir->info.stage].image_index; in set_image_access()
146 pipeline->access[nir->info.stage].images_read |= mask; in set_image_access()
148 pipeline->access[nir->info.stage].images_written |= mask; in set_image_access()
152 set_buffer_access(struct lvp_pipeline *pipeline, nir_shader *nir, in set_buffer_access() argument
161 var = nir_get_binding_variable(nir, b); in set_buffer_access()
173 value += get_set_layout(pipeline->layout, s)->stage[nir->info.stage].shader_buffer_count; in set_buffer_access()
175 value += binding->stage[nir->info.stage].shader_buffer_index; in set_buffer_access()
179 pipeline->access[nir->info.stage].buffers_written |= mask; in set_buffer_access()
[all …]
|
| /third_party/mesa3d/src/gallium/auxiliary/nir/ |
| D | nir_to_tgsi_info.c | 135 static void gather_intrinsic_load_deref_info(const nir_shader *nir, in gather_intrinsic_load_deref_info() argument
144 if (nir->info.stage == MESA_SHADER_FRAGMENT) in gather_intrinsic_load_deref_info()
148 switch (nir->info.stage) { in gather_intrinsic_load_deref_info()
170 static void scan_instruction(const struct nir_shader *nir, in scan_instruction() argument
343 gather_intrinsic_load_deref_info(nir, intr, deref, need_texcoord, var, info); in scan_instruction()
407 void nir_tgsi_scan_shader(const struct nir_shader *nir, in nir_tgsi_scan_shader() argument
413 info->processor = pipe_shader_type_from_mesa(nir->info.stage); in nir_tgsi_scan_shader()
418 pipe_shader_type_from_mesa(nir->info.next_stage); in nir_tgsi_scan_shader()
420 if (nir->info.stage == MESA_SHADER_VERTEX) { in nir_tgsi_scan_shader()
422 nir->info.vs.window_space_position; in nir_tgsi_scan_shader()
[all …]
|
| /third_party/mesa3d/src/panfrost/vulkan/ |
| D | panvk_vX_shader.c | 96 nir_shader *nir, in panvk_lower_blend() argument
163 NIR_PASS_V(nir, nir_lower_blend, &options); in panvk_lower_blend()
172 NIR_PASS_V(nir, nir_shader_instructions_pass, in panvk_lower_blend()
250 nir_shader *nir; in panvk_per_arch() local
256 NULL, &nir); in panvk_per_arch()
262 NIR_PASS_V(nir, nir_lower_io_to_temporaries, in panvk_per_arch()
263 nir_shader_get_entrypoint(nir), true, true); in panvk_per_arch()
276 NIR_PASS_V(nir, nir_lower_indirect_derefs, in panvk_per_arch()
280 NIR_PASS_V(nir, nir_opt_copy_prop_vars); in panvk_per_arch()
281 NIR_PASS_V(nir, nir_opt_combine_stores, nir_var_all); in panvk_per_arch()
[all …]
|