Home
last modified time | relevance | path

Searched refs:nir (Results 1 - 25 of 285) sorted by relevance

12345678910>>...12

/third_party/mesa3d/src/gallium/drivers/radeonsi/
H A Dsi_shader_nir.c57 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_continue in si_nir_opts()
137 si_nir_late_opts(nir_shader *nir) si_nir_late_opts() argument
158 si_late_optimize_16bit_samplers(struct si_screen *sscreen, nir_shader *nir) si_late_optimize_16bit_samplers() argument
228 si_lower_intrinsics(nir_shader *nir) si_lower_intrinsics() argument
240 si_lower_nir(struct si_screen *sscreen, struct nir_shader *nir) si_lower_nir() argument
334 struct nir_shader *nir = (struct nir_shader *)nirptr; si_finalize_nir() local
[all...]
H A Dsi_shader_info.c173 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 in scan_instruction()
582 si_nir_scan_shader(struct si_screen *sscreen, const struct nir_shader *nir, struct si_shader_info *info) si_nir_scan_shader() argument
[all...]
/third_party/mesa3d/src/compiler/nir/
H A Dnir_sweep.c24 #include "nir.h"
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_loo argument
88 sweep_cf_node(nir_shader *nir, nir_cf_node *cf_node) sweep_cf_node() argument
106 sweep_impl(nir_shader *nir, nir_function_impl *impl) sweep_impl() argument
124 sweep_function(nir_shader *nir, nir_function *f) sweep_function() argument
134 nir_sweep(nir_shader *nir) nir_sweep() argument
[all...]
H A Dnir_lower_clip_cull_distance_arrays.c24 #include "nir.h"
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 in combine_clip_cull()
128 nir_lower_clip_cull_distance_arrays(nir_shader *nir) nir_lower_clip_cull_distance_arrays() argument
[all...]
/third_party/mesa3d/src/gallium/drivers/lima/standalone/
H A Dlima_compiler_cmdline.c62 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()
220 nir_shader *nir = load_glsl(1, filename, stage); main() local
[all...]
/third_party/mesa3d/src/imagination/rogue/
H A Drogue_nir.c25 #include "nir/nir.h"
26 #include "nir/nir_schedule.h"
78 nir_shader *nir, in rogue_nir_passes()
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_scala in rogue_nir_passes()
77 rogue_nir_passes(struct rogue_build_ctx *ctx, nir_shader *nir, gl_shader_stage stage) rogue_nir_passes() argument
[all...]
/third_party/mesa3d/src/gallium/drivers/freedreno/ir3/
H A Dir3_cmdline.c37 #include "nir/tgsi_to_nir.h"
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_temporarie in load_glsl()
244 nir_shader *nir; load_spirv() local
369 nir_shader *nir; main() local
[all...]
/third_party/mesa3d/src/mesa/state_tracker/
H A Dst_glsl_to_nir.cpp45 #include "compiler/nir/nir.h"
46 #include "compiler/nir/nir_builder.h"
63 * may need to fix up varying slots so the glsl->nir path is aligned
64 * with the anything->tgsi->nir path.
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 in st_nir_assign_vs_in_locations()
178 st_nir_assign_uniform_locations(struct gl_context *ctx, struct gl_program *prog, nir_shader *nir) st_nir_assign_uniform_locations() argument
236 st_nir_add_point_size(nir_shader *nir) st_nir_add_point_size() argument
310 st_nir_zero_initialize_clip_distance(nir_shader *nir) st_nir_zero_initialize_clip_distance() argument
340 nir_shader *nir = prog->nir; st_nir_preprocess() local
467 nir_shader *nir = prog->nir; st_glsl_to_nir_post_opts() local
643 st_nir_lower_wpos_ytransform(struct nir_shader *nir, struct gl_program *prog, struct pipe_screen *pscreen) st_nir_lower_wpos_ytransform() argument
777 nir_shader *nir = shader->Program->nir; st_link_nir() local
933 st_nir_assign_varying_locations(struct st_context *st, nir_shader *nir) st_nir_assign_varying_locations() argument
968 st_nir_lower_samplers(struct pipe_screen *screen, nir_shader *nir, struct gl_shader_program *shader_program, struct gl_program *prog) st_nir_lower_samplers() argument
1000 st_nir_lower_uniforms(struct st_context *st, nir_shader *nir) st_nir_lower_uniforms() argument
1022 st_finalize_nir(struct st_context *st, struct gl_program *prog, struct gl_shader_program *shader_program, nir_shader *nir, bool finalize_by_driver, bool is_before_variants) st_finalize_nir() argument
[all...]
H A Dst_program.c45 #include "compiler/nir/nir.h"
46 #include "compiler/nir/nir_serialize.h"
56 #include "nir/nir_to_tgsi.h"
330 /* Note: Any setup of ->ir.nir that has had pipe->create_*_state called on in st_release_variants()
332 * callers should be NULLing out the nir field in any pipe_shader_state in st_release_variants()
335 * GLSL IR and ARB programs will have set gl_program->nir to the same in st_release_variants()
336 * shader as ir->ir.nir, so it will be freed by _mesa_delete_program(). in st_release_variants()
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_copie in st_finalize_nir_before_variants()
374 st_prog_to_nir_postprocess(struct st_context *st, nir_shader *nir, struct gl_program *prog) st_prog_to_nir_postprocess() argument
418 nir_shader *nir = prog_to_nir(st->ctx, prog, options); st_translate_prog_to_nir() local
504 nir_shader *nir = state->ir.nir; st_create_nir_shader() local
615 nir_shader *nir = prog->nir; get_nir_shader() local
635 lower_ucp(struct st_context *st, struct nir_shader *nir, unsigned ucp_enables, struct gl_program_parameter_list *params) lower_ucp() argument
854 nir_shader *nir = st_translate_fragment_program() local
1226 nir_shader *nir = prog->nir; st_can_add_pointsize_to_program() local
[all...]
H A Dst_nir_builtins.c27 #include "compiler/nir/nir_builder.h"
34 nir_shader *nir) in st_nir_finish_builtin_shader()
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_value in st_nir_finish_builtin_shader()
33 st_nir_finish_builtin_shader(struct st_context *st, nir_shader *nir) st_nir_finish_builtin_shader() argument
[all...]
/third_party/mesa3d/src/amd/vulkan/
H A Dradv_shader_info.c23 #include "nir/nir.h"
24 #include "nir/nir_xfb_info.h"
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, inst in gather_intrinsic_info()
212 gather_tex_info(const nir_shader *nir, const nir_tex_instr *instr, struct radv_shader_info *info) gather_tex_info() argument
229 gather_info_block(const nir_shader *nir, const nir_block *block, struct radv_shader_info *info) gather_info_block() argument
246 gather_info_input_decl_vs(const nir_shader *nir, const nir_variable *var, const struct radv_pipeline_key *key, struct radv_shader_info *info) gather_info_input_decl_vs() argument
288 gather_info_input_decl_ps(const nir_shader *nir, const nir_variable *var, struct radv_shader_info *info) gather_info_input_decl_ps() argument
328 gather_info_input_decl(const nir_shader *nir, const nir_variable *var, const struct radv_pipeline_key *key, struct radv_shader_info *info) gather_info_input_decl() argument
344 gather_info_output_decl_gs(const nir_shader *nir, const nir_variable *var, struct radv_shader_info *info) gather_info_output_decl_gs() argument
358 get_vs_output_info(const nir_shader *nir, struct radv_shader_info *info) get_vs_output_info() argument
383 gather_info_output_decl(const nir_shader *nir, const nir_variable *var, struct radv_shader_info *info) gather_info_output_decl() argument
400 gather_xfb_info(const nir_shader *nir, struct radv_shader_info *info) gather_xfb_info() argument
457 radv_nir_shader_info_pass(struct radv_device *device, const struct nir_shader *nir, const struct radv_pipeline_layout *layout, const struct radv_pipeline_key *pipeline_key, struct radv_shader_info *info) radv_nir_shader_info_pass() argument
[all...]
/third_party/mesa3d/src/microsoft/spirv_to_dxil/
H A Ddxil_spirv_nir.c48 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_i in dxil_spirv_nir_link()
580 dxil_spirv_nir_passes(nir_shader *nir, const struct dxil_spirv_runtime_conf *conf, bool *requires_runtime_data) dxil_spirv_nir_passes() argument
[all...]
H A Dspirv_to_dxil.c52 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_copie in spirv_to_dxil_nir_prep()
126 nir_shader *nir = spirv_to_nir( spirv_to_dxil() local
[all...]
/third_party/mesa3d/src/microsoft/clc/
H A Dclc_compiler.c24 #include "nir.h"
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_ub in add_kernel_inputs_var()
425 add_work_properties_var(struct clc_dxil_object *dxil, struct nir_shader *nir, unsigned *cbv_id) add_work_properties_var() argument
443 clc_lower_constant_to_ssbo(nir_shader *nir, const struct clc_kernel_info *kerninfo, unsigned *uav_id) clc_lower_constant_to_ssbo() argument
481 clc_lower_global_to_ssbo(nir_shader *nir) clc_lower_global_to_ssbo() argument
695 shader_has_double(nir_shader *nir) shader_has_double() argument
743 struct nir_shader *nir; clc_spirv_to_dxil() local
[all...]
/third_party/mesa3d/src/gallium/frontends/clover/nir/
H A Dinvocation.cpp35 #include <compiler/nir/nir_builder.h>
36 #include <compiler/nir/nir_serialize.h>
345 clover_lower_nir(nir_shader *nir, std::vector<binary::argument> &args,
349 if (nir->constant_data_size) {
352 constant_var = nir_variable_create(nir, nir_var_uniform, type,
363 return nir_shader_lower_instructions(nir,
397 struct disk_cache *clover::nir::create_clc_disk_cache(void)
404 if (!disk_cache_get_function_identifier((void *)clover::nir::create_clc_disk_cache, &ctx))
413 void clover::nir::check_for_libclc(const device &dev)
419 nir_shader *clover::nir
[all...]
/third_party/mesa3d/src/intel/compiler/
H A Dbrw_kernel.c27 #include "compiler/nir/nir_builder.h"
40 nir_shader *nir = nir_load_libclc_shader(64, disk_cache, in load_clc_shader()
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
304 nir_shader *nir = brw_kernel_from_spirv() local
[all...]
H A Dbrw_nir.h28 #include "compiler/nir/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);
[all...]
H A Dbrw_nir.c29 #include "compiler/nir/nir_builder.h"
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 in brw_nir_lower_vs_inputs()
298 brw_nir_lower_vue_inputs(nir_shader *nir, const struct brw_vue_map *vue_map) brw_nir_lower_vue_inputs() argument
351 brw_nir_lower_tes_inputs(nir_shader *nir, const struct brw_vue_map *vue_map) brw_nir_lower_tes_inputs() argument
416 brw_nir_lower_fs_inputs(nir_shader *nir, const struct intel_device_info *devinfo, const struct brw_wm_prog_key *key) brw_nir_lower_fs_inputs() argument
470 brw_nir_lower_vue_outputs(nir_shader *nir) brw_nir_lower_vue_outputs() argument
481 brw_nir_lower_tcs_outputs(nir_shader *nir, const struct brw_vue_map *vue_map, enum tess_primitive_mode tes_primitive_mode) brw_nir_lower_tcs_outputs() argument
508 brw_nir_lower_fs_outputs(nir_shader *nir) brw_nir_lower_fs_outputs() argument
528 brw_nir_optimize(nir_shader *nir, const struct brw_compiler *compiler, bool is_scalar, bool allow_copies) brw_nir_optimize() argument
812 brw_preprocess_nir(const struct brw_compiler *compiler, nir_shader *nir, const nir_shader *softfp64) brw_preprocess_nir() argument
1083 brw_vectorize_lower_mem_access(nir_shader *nir, const struct brw_compiler *compiler, bool is_scalar, bool robust_buffer_access) brw_vectorize_lower_mem_access() argument
1123 nir_shader_has_local_variables(const nir_shader *nir) nir_shader_has_local_variables() argument
1141 brw_postprocess_nir(nir_shader *nir, const struct brw_compiler *compiler, bool is_scalar, bool debug_enabled, bool robust_buffer_access) brw_postprocess_nir() argument
1324 brw_nir_apply_sampler_key(nir_shader *nir, const struct brw_compiler *compiler, const struct brw_sampler_prog_key_data *key_tex) brw_nir_apply_sampler_key() argument
1416 brw_nir_apply_key(nir_shader *nir, const struct brw_compiler *compiler, const struct brw_base_prog_key *key, unsigned max_subgroup_size, bool is_scalar) brw_nir_apply_key() argument
1604 nir_shader *nir = b.shader; brw_nir_create_passthrough_tcs() local
[all...]
H A Dbrw_nir_lower_cs_intrinsics.c25 #include "compiler/nir/nir_builder.h"
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 in lower_cs_intrinsics_convert_block()
274 brw_nir_lower_cs_intrinsics(nir_shader *nir) brw_nir_lower_cs_intrinsics() argument
[all...]
/third_party/mesa3d/src/asahi/compiler/
H A Dcmdline.c60 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[ in compile_shader()
[all...]
/third_party/mesa3d/src/vulkan/runtime/
H A Dvk_nir.c27 #include "compiler/nir/nir_xfb_info.h"
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_function in vk_spirv_to_nir()
[all...]
/third_party/mesa3d/src/gallium/frontends/lavapipe/
H A Dlvp_pipeline.c31 #include "nir/nir_builder.h"
36 #include "nir/nir_xfb_info.h"
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 in set_buffer_access()
183 scan_intrinsic(struct lvp_pipeline *pipeline, nir_shader *nir, nir_intrinsic_instr *instr) scan_intrinsic() argument
230 scan_pipeline_info(struct lvp_pipeline *pipeline, nir_shader *nir) scan_pipeline_info() argument
262 remove_scoped_barriers(nir_shader *nir, bool is_compute) remove_scoped_barriers() argument
285 lower_demote(nir_shader *nir) lower_demote() argument
324 optimize(nir_shader *nir) optimize() argument
373 lvp_shader_optimize(nir_shader *nir) lvp_shader_optimize() argument
390 nir_shader *nir; lvp_shader_compile_to_ir() local
614 lvp_pipeline_compile_stage(struct lvp_pipeline *pipeline, nir_shader *nir) lvp_pipeline_compile_stage() argument
650 lvp_pipeline_compile(struct lvp_pipeline *pipeline, nir_shader *nir) lvp_pipeline_compile() argument
[all...]
/third_party/mesa3d/src/panfrost/bifrost/
H A Dcmdline.c93 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[ in compile_shader()
[all...]
/third_party/mesa3d/src/gallium/auxiliary/nir/
H A Dnir_to_tgsi_info.c33 #include "nir.h"
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 in nir_tgsi_scan_shader()
[all...]
/third_party/mesa3d/src/panfrost/vulkan/
H A Dpanvk_vX_shader.c96 nir_shader *nir, in panvk_lower_blend()
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 shader_create() local
256 NULL, &nir); in shader_create()
262 NIR_PASS_V(nir, nir_lower_io_to_temporaries, in shader_create()
263 nir_shader_get_entrypoint(nir), true, true); in shader_create()
276 NIR_PASS_V(nir, nir_lower_indirect_derefs, in shader_create()
280 NIR_PASS_V(nir, nir_opt_copy_prop_vars); in shader_create()
281 NIR_PASS_V(nir, nir_opt_combine_store in shader_create()
95 panvk_lower_blend(struct panfrost_device *pdev, nir_shader *nir, struct panfrost_compile_inputs *inputs, struct pan_blend_state *blend_state, bool static_blend_constants) panvk_lower_blend() argument
[all...]

Completed in 18 milliseconds

12345678910>>...12