| /aosp_15_r20/external/mesa3d/src/intel/compiler/elk/ |
| H A D | elk_nir.c | 239 elk_nir_lower_vs_inputs(nir_shader *nir, in elk_nir_lower_vs_inputs()
368 elk_nir_lower_vue_inputs(nir_shader *nir, in elk_nir_lower_vue_inputs()
418 elk_nir_lower_tes_inputs(nir_shader *nir, const struct intel_vue_map *vue_map) in elk_nir_lower_tes_inputs()
492 elk_nir_lower_fs_inputs(nir_shader *nir, in elk_nir_lower_fs_inputs()
545 elk_nir_lower_vue_outputs(nir_shader *nir) in elk_nir_lower_vue_outputs()
556 elk_nir_lower_tcs_outputs(nir_shader *nir, const struct intel_vue_map *vue_map, in elk_nir_lower_tcs_outputs()
580 elk_nir_lower_fs_outputs(nir_shader *nir) in elk_nir_lower_fs_outputs()
600 elk_nir_optimize(nir_shader *nir, bool is_scalar, in elk_nir_optimize()
880 elk_preprocess_nir(const struct elk_compiler *compiler, nir_shader *nir, in elk_preprocess_nir()
1284 elk_vectorize_lower_mem_access(nir_shader *nir, in elk_vectorize_lower_mem_access()
[all …]
|
| /aosp_15_r20/external/mesa3d/src/amd/vulkan/ |
| H A D | radv_shader_info.c | 24 radv_use_vs_prolog(const nir_shader *nir, in radv_use_vs_prolog()
31 radv_use_per_attribute_vb_descs(const nir_shader *nir, in radv_use_per_attribute_vb_descs()
39 gather_load_vs_input_info(const nir_shader *nir, const nir_intrinsic_instr *intrin, struct radv_sha… in gather_load_vs_input_info()
67 gather_load_fs_input_info(const nir_shader *nir, const nir_intrinsic_instr *intrin, struct radv_sha… in gather_load_fs_input_info()
117 gather_intrinsic_load_input_info(const nir_shader *nir, const nir_intrinsic_instr *instr, struct ra… in gather_intrinsic_load_input_info()
134 gather_intrinsic_store_output_info(const nir_shader *nir, const nir_intrinsic_instr *instr, in gather_intrinsic_store_output_info()
193 gather_push_constant_info(const nir_shader *nir, const nir_intrinsic_instr *instr, struct radv_shad… in gather_push_constant_info()
211 gather_intrinsic_info(const nir_shader *nir, const nir_intrinsic_instr *instr, struct radv_shader_i… in gather_intrinsic_info()
320 gather_tex_info(const nir_shader *nir, const nir_tex_instr *instr, struct radv_shader_info *info) in gather_tex_info()
337 gather_info_block(const nir_shader *nir, const nir_block *block, struct radv_shader_info *info, in gather_info_block()
[all …]
|
| /aosp_15_r20/external/mesa3d/src/intel/compiler/ |
| H A D | brw_nir.c | 346 brw_nir_lower_vs_inputs(nir_shader *nir) in brw_nir_lower_vs_inputs()
463 brw_nir_lower_vue_inputs(nir_shader *nir, in brw_nir_lower_vue_inputs()
513 brw_nir_lower_tes_inputs(nir_shader *nir, const struct intel_vue_map *vue_map) in brw_nir_lower_tes_inputs()
587 brw_nir_lower_fs_inputs(nir_shader *nir, in brw_nir_lower_fs_inputs()
634 brw_nir_lower_vue_outputs(nir_shader *nir) in brw_nir_lower_vue_outputs()
645 brw_nir_lower_tcs_outputs(nir_shader *nir, const struct intel_vue_map *vue_map, in brw_nir_lower_tcs_outputs()
669 brw_nir_lower_fs_outputs(nir_shader *nir) in brw_nir_lower_fs_outputs()
696 brw_nir_tag_speculative_access(nir_shader *nir) in brw_nir_tag_speculative_access()
734 brw_nir_optimize(nir_shader *nir, in brw_nir_optimize()
1010 brw_preprocess_nir(const struct brw_compiler *compiler, nir_shader *nir, in brw_preprocess_nir()
[all …]
|
| H A D | brw_compile_mesh.cpp | 73 brw_nir_lower_load_uniforms(nir_shader *nir) in brw_nir_lower_load_uniforms()
138 brw_nir_lower_launch_mesh_workgroups(nir_shader *nir) in brw_nir_lower_launch_mesh_workgroups()
147 brw_nir_lower_tue_outputs(nir_shader *nir, brw_tue_map *map) in brw_nir_lower_tue_outputs()
216 brw_nir_adjust_task_payload_offsets(nir_shader *nir) in brw_nir_adjust_task_payload_offsets()
255 brw_nir_align_launch_mesh_workgroups(nir_shader *nir) in brw_nir_align_launch_mesh_workgroups()
329 struct nir_shader *nir = params->base.nir; in brw_compile_task() local
439 brw_nir_lower_tue_inputs(nir_shader *nir, const brw_tue_map *map) in brw_nir_lower_tue_inputs()
558 struct nir_shader *nir, in brw_compute_mue_layout()
826 struct nir_shader *nir, struct brw_mue_map *map, in brw_compute_mue_map()
1138 brw_print_mue_map(FILE *fp, const struct brw_mue_map *map, struct nir_shader *nir) in brw_print_mue_map()
[all …]
|
| H A D | brw_nir_rt.c | 192 lower_rt_io_and_scratch(nir_shader *nir) in lower_rt_io_and_scratch()
344 brw_nir_lower_raygen(nir_shader *nir) in brw_nir_lower_raygen()
352 brw_nir_lower_any_hit(nir_shader *nir, const struct intel_device_info *devinfo) in brw_nir_lower_any_hit()
361 brw_nir_lower_closest_hit(nir_shader *nir) in brw_nir_lower_closest_hit()
369 brw_nir_lower_miss(nir_shader *nir) in brw_nir_lower_miss()
377 brw_nir_lower_callable(nir_shader *nir) in brw_nir_lower_callable()
492 nir_shader *nir = b.shader; in brw_nir_create_raygen_trampoline() local
|
| H A D | brw_kernel.c | 46 nir_shader *nir = nir_load_libclc_shader(64, disk_cache, in load_clc_shader() local
126 implement_intel_builtins(nir_shader *nir) in implement_intel_builtins()
163 lower_kernel_intrinsics(nir_shader *nir) in lower_kernel_intrinsics()
306 nir_shader *nir = in brw_kernel_from_spirv() local
503 nir_remove_llvm17_scratch(nir_shader *nir) in nir_remove_llvm17_scratch()
570 cleanup_llvm17_scratch(nir_shader *nir) in cleanup_llvm17_scratch()
621 nir_shader *nir = in brw_nir_from_spirv() local
|
| /aosp_15_r20/external/mesa3d/src/compiler/nir/ |
| H A D | nir_sweep.c | 46 sweep_block(nir_shader *nir, nir_block *block) in sweep_block()
80 sweep_if(nir_shader *nir, nir_if *iff) in sweep_if()
94 sweep_loop(nir_shader *nir, nir_loop *loop) in sweep_loop()
105 sweep_cf_node(nir_shader *nir, nir_cf_node *cf_node) in sweep_cf_node()
123 sweep_impl(nir_shader *nir, nir_function_impl *impl) in sweep_impl()
140 sweep_function(nir_shader *nir, nir_function *f) in sweep_function()
150 nir_sweep(nir_shader *nir) in nir_sweep()
|
| /aosp_15_r20/external/mesa3d/src/nouveau/compiler/ |
| H A D | nak_nir.c | 13 #define OPT(nir, pass, ...) ({ \ argument
21 #define OPT_V(nir, pass, ...) NIR_PASS_V(nir, pass, ##__VA_ARGS__) argument
24 nak_nir_workgroup_has_one_subgroup(const nir_shader *nir) in nak_nir_workgroup_has_one_subgroup()
92 optimize_nir(nir_shader *nir, const struct nak_compiler *nak, bool allow_copies) in optimize_nir()
177 nak_optimize_nir(nir_shader *nir, const struct nak_compiler *nak) in nak_optimize_nir()
292 nak_preprocess_nir(nir_shader *nir, const struct nak_compiler *nak) in nak_preprocess_nir()
632 nak_nir_lower_system_values(nir_shader *nir, const struct nak_compiler *nak) in nak_nir_lower_system_values()
703 nak_nir_lower_fs_outputs(nir_shader *nir) in nak_nir_lower_fs_outputs()
765 nak_nir_remove_barriers(nir_shader *nir) in nak_nir_remove_barriers()
858 nir_shader_has_local_variables(const nir_shader *nir) in nir_shader_has_local_variables()
[all …]
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/radeonsi/ |
| H A D | si_shader_nir.c | 78 void si_nir_opts(struct si_screen *sscreen, struct nir_shader *nir, bool first) in si_nir_opts()
163 void si_nir_late_opts(nir_shader *nir) in si_nir_late_opts()
184 static void si_late_optimize_16bit_samplers(struct si_screen *sscreen, nir_shader *nir) in si_late_optimize_16bit_samplers()
257 static bool si_lower_intrinsics(nir_shader *nir) in si_lower_intrinsics()
265 void si_lower_mediump_io(nir_shader *nir) in si_lower_mediump_io()
280 static void si_lower_nir(struct si_screen *sscreen, struct nir_shader *nir) in si_lower_nir()
374 static bool si_mark_divergent_texture_non_uniform(struct nir_shader *nir) in si_mark_divergent_texture_non_uniform()
432 struct nir_shader *nir = (struct nir_shader *)nirptr; in si_finalize_nir() local
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/etnaviv/ |
| H A D | etnaviv_compiler_nir_emit.c | 41 #define OPCT(nir, op, cond, type) [nir_op_##nir] = { \ argument
46 #define OPC(nir, op, cond) OPCT(nir, op, cond, F32) argument
47 #define IOPC(nir, op, cond) OPCT(nir, op, cond, S32) argument
48 #define UOPC(nir, op, cond) OPCT(nir, op, cond, U32) argument
49 #define OP(nir, op) OPC(nir, op, TRUE) argument
50 #define IOP(nir, op) IOPC(nir, op, TRUE) argument
51 #define UOP(nir, op) UOPC(nir, op, TRUE) argument
|
| /aosp_15_r20/external/mesa3d/src/mesa/state_tracker/ |
| H A D | st_glsl_to_nir.cpp | 98 st_nir_assign_vs_in_locations(struct nir_shader *nir) in st_nir_assign_vs_in_locations()
184 nir_shader *nir) in st_nir_assign_uniform_locations()
279 nir_shader *nir = prog->nir; in st_glsl_to_nir_post_opts() local
449 st_nir_lower_wpos_ytransform(struct nir_shader *nir, in st_nir_lower_wpos_ytransform()
600 nir_shader *nir = shader->Program->nir; in st_link_glsl_to_nir() local
788 st_nir_assign_varying_locations(struct st_context *st, nir_shader *nir) in st_nir_assign_varying_locations()
827 st_nir_lower_samplers(struct pipe_screen *screen, nir_shader *nir, in st_nir_lower_samplers()
859 st_nir_lower_uniforms(struct st_context *st, nir_shader *nir) in st_nir_lower_uniforms()
883 nir_shader *nir, bool finalize_by_driver, in st_finalize_nir()
|
| H A D | st_program.c | 347 st_finalize_nir_before_variants(struct nir_shader *nir) in st_finalize_nir_before_variants()
367 st_prog_to_nir_postprocess(struct st_context *st, nir_shader *nir, in st_prog_to_nir_postprocess()
418 nir_shader *nir = prog_to_nir(st->ctx, prog, options); in st_translate_prog_to_nir() local
506 nir_shader *nir = state->ir.nir; in st_create_nir_shader() local
638 nir_shader *nir = prog->nir; in get_nir_shader() local
666 struct nir_shader *nir, in lower_ucp()
1369 st_serialize_base_nir(struct gl_program *prog, nir_shader *nir) in st_serialize_base_nir()
|
| /aosp_15_r20/external/mesa3d/src/freedreno/ir3/ |
| H A D | ir3_nir_analyze_ubo_ranges.c | 13 get_ubo_load_range(nir_shader *nir, nir_intrinsic_instr *instr, in get_ubo_load_range()
136 gather_ubo_ranges(nir_shader *nir, nir_intrinsic_instr *instr, in gather_ubo_ranges()
343 rematerialize_load_global_bases(nir_shader *nir, in rematerialize_load_global_bases()
376 copy_global_to_uniform(nir_shader *nir, struct ir3_ubo_analysis_state *state) in copy_global_to_uniform()
431 copy_ubo_to_uniform(nir_shader *nir, const struct ir3_const_state *const_state, in copy_ubo_to_uniform()
547 ir3_nir_lower_const_global_loads(nir_shader *nir, struct ir3_shader_variant *v) in ir3_nir_lower_const_global_loads()
622 ir3_nir_analyze_ubo_ranges(nir_shader *nir, struct ir3_shader_variant *v) in ir3_nir_analyze_ubo_ranges()
669 ir3_nir_lower_ubo_loads(nir_shader *nir, struct ir3_shader_variant *v) in ir3_nir_lower_ubo_loads()
785 ir3_nir_fixup_load_const_ir3(nir_shader *nir) in ir3_nir_fixup_load_const_ir3()
839 ir3_nir_lower_load_constant(nir_shader *nir, struct ir3_shader_variant *v) in ir3_nir_lower_load_constant()
|
| /aosp_15_r20/external/mesa3d/src/gallium/frontends/lavapipe/ |
| H A D | lvp_pipeline.c | 162 remove_barriers(nir_shader *nir, bool is_compute) in remove_barriers()
184 lower_demote(nir_shader *nir) in lower_demote()
224 optimize(nir_shader *nir) in optimize()
273 lvp_shader_optimize(nir_shader *nir) in lvp_shader_optimize()
283 lvp_create_pipeline_nir(nir_shader *nir) in lvp_create_pipeline_nir()
295 nir_shader **nir) in compile_spirv()
353 lvp_shader_lower(struct lvp_device *pdevice, struct lvp_pipeline *pipeline, nir_shader *nir, struct… in lvp_shader_lower()
486 lvp_shader_init(struct lvp_shader *shader, nir_shader *nir) in lvp_shader_init()
502 nir_shader *nir; in lvp_shader_compile_to_ir() local
597 lvp_shader_compile_stage(struct lvp_device *device, struct lvp_shader *shader, nir_shader *nir) in lvp_shader_compile_stage()
[all …]
|
| H A D | lvp_lower_exec_graph.c | 65 lvp_lower_node_payload_derefs(nir_shader *nir) in lvp_lower_node_payload_derefs()
124 lvp_lower_exec_graph_intrinsics(nir_shader *nir) in lvp_lower_exec_graph_intrinsics()
131 lvp_lower_node_payload_vars(struct lvp_pipeline *pipeline, nir_shader *nir) in lvp_lower_node_payload_vars()
150 lvp_lower_exec_graph(struct lvp_pipeline *pipeline, nir_shader *nir) in lvp_lower_exec_graph()
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/zink/ |
| H A D | zink_compiler.c | 90 create_gfx_pushconst(nir_shader *nir) in create_gfx_pushconst()
1077 nir_shader *nir = b.shader; in zink_create_quads_emulation_gs() local
1202 zink_lower_system_values_to_inlined_uniforms(nir_shader *nir) in zink_lower_system_values_to_inlined_uniforms()
1816 find_var_with_location_frac(nir_shader *nir, unsigned location, unsigned location_frac, bool have_p… in find_var_with_location_frac()
1846 update_psiz_location(nir_shader *nir, nir_variable *psiz) in update_psiz_location()
1929 get_var_slot_count(nir_shader *nir, nir_variable *var) in get_var_slot_count()
1959 update_so_info(struct zink_shader *zs, nir_shader *nir, uint64_t outputs_written, bool have_psiz) in update_so_info()
2128 decompose_attribs(nir_shader *nir, uint32_t decomposed_attrs, uint32_t decomposed_attrs_without_w) in decompose_attribs()
2501 find_var_deref(nir_shader *nir, nir_variable *var) in find_var_deref()
2518 find_var_io(nir_shader *nir, nir_variable *var) in find_var_io()
[all …]
|
| /aosp_15_r20/external/mesa3d/src/nouveau/vulkan/ |
| H A D | nvk_codegen.c | 106 nvk_cg_preprocess_nir(nir_shader *nir) in nvk_cg_preprocess_nir()
130 nvk_cg_optimize_nir(nir_shader *nir) in nvk_cg_optimize_nir()
224 assign_io_locations(nir_shader *nir) in assign_io_locations()
259 nak_cg_postprocess_nir(nir_shader *nir) in nak_cg_postprocess_nir()
528 const struct nir_shader *nir, in nvk_gs_gen_header()
738 static uint8_t find_register_index_for_xfb_output(const struct nir_shader *nir, in find_register_index_for_xfb_output()
755 struct nir_shader *nir, in nvk_fill_transform_feedback_state()
796 nvk_cg_compile_nir(struct nvk_physical_device *pdev, nir_shader *nir, in nvk_cg_compile_nir()
|
| /aosp_15_r20/external/mesa3d/src/compiler/glsl/ |
| H A D | gl_nir_linker.c | 46 gl_nir_opts(nir_shader *nir) in gl_nir_opts()
396 nir_shader *nir = prog->nir; in gl_nir_can_add_pointsize_to_program() local
804 nir_shader *nir, nir_variable_mode modes, in add_vars_with_modes()
893 nir_shader *nir = sh->Program->nir; in add_interface_variables() local
1136 remove_dead_varyings_pre_linking(nir_shader *nir) in remove_dead_varyings_pre_linking()
1151 gl_nir_add_point_size(nir_shader *nir) in gl_nir_add_point_size()
1207 gl_nir_zero_initialize_clip_distance(nir_shader *nir) in gl_nir_zero_initialize_clip_distance()
1259 nir_shader *nir = prog->nir; in preprocess_shader() local
1395 nir_shader *nir = linked_shader[i]->Program->nir; in prelink_lowering() local
1418 get_varying_nir_var_mask(nir_shader *nir) in get_varying_nir_var_mask()
[all …]
|
| /aosp_15_r20/external/mesa3d/src/microsoft/spirv_to_dxil/ |
| H A D | dxil_spirv_nir.c | 113 dxil_spirv_nir_prep(nir_shader *nir) in dxil_spirv_nir_prep()
189 add_runtime_data_var(nir_shader *nir, unsigned desc_set, unsigned binding) in add_runtime_data_var()
308 add_push_constant_var(nir_shader *nir, unsigned size, unsigned desc_set, unsigned binding) in add_push_constant_var()
637 dxil_spirv_write_pntc(nir_shader *nir, const struct dxil_spirv_runtime_conf *conf) in dxil_spirv_write_pntc()
693 dxil_spirv_compute_pntc(nir_shader *nir) in dxil_spirv_compute_pntc()
746 lower_view_index_to_rt_layer(nir_shader *nir) in lower_view_index_to_rt_layer()
773 dxil_spirv_nir_link(nir_shader *nir, nir_shader *prev_stage_nir, in dxil_spirv_nir_link()
838 merge_ubos_and_ssbos(nir_shader *nir) in merge_ubos_and_ssbos()
887 dxil_spirv_nir_passes(nir_shader *nir, in dxil_spirv_nir_passes()
|
| /aosp_15_r20/external/mesa3d/src/microsoft/clc/ |
| H A D | clc_compiler.c | 276 clc_lower_images(nir_shader *nir, struct clc_image_lower_context *context) in clc_lower_images()
306 clc_lower_64bit_semantics(nir_shader *nir) in clc_lower_64bit_semantics()
345 clc_lower_nonnormalized_samplers(nir_shader *nir, in clc_lower_nonnormalized_samplers()
414 add_kernel_inputs_var(struct clc_dxil_object *dxil, nir_shader *nir, in add_kernel_inputs_var()
442 struct nir_shader *nir, unsigned *cbv_id) in add_work_properties_var()
459 clc_lower_constant_to_ssbo(nir_shader *nir, in clc_lower_constant_to_ssbo()
494 clc_change_variable_mode(nir_shader *nir, nir_variable_mode from, nir_variable_mode to) in clc_change_variable_mode()
581 static bool shader_has_double(nir_shader *nir) in shader_has_double()
730 struct nir_shader *nir; in clc_spirv_to_dxil() local
|
| H A D | clc_nir.c | 99 clc_nir_lower_system_values(nir_shader *nir, nir_variable *var) in clc_nir_lower_system_values()
181 clc_nir_lower_kernel_input_loads(nir_shader *nir, nir_variable *var) in clc_nir_lower_kernel_input_loads()
210 add_printf_var(struct nir_shader *nir, unsigned uav_id) in add_printf_var()
224 clc_lower_printf_base(nir_shader *nir, unsigned uav_id) in clc_lower_printf_base()
333 clc_nir_lower_global_pointers_to_constants(nir_shader *nir) in clc_nir_lower_global_pointers_to_constants()
|
| /aosp_15_r20/external/mesa3d/src/asahi/vulkan/ |
| H A D | hk_shader.c | 118 hk_preprocess_nir_internal(struct vk_physical_device *vk_pdev, nir_shader *nir) in hk_preprocess_nir_internal()
173 hk_preprocess_nir(struct vk_physical_device *vk_pdev, nir_shader *nir) in hk_preprocess_nir()
328 nir_has_image_var(nir_shader *nir) in nir_has_image_var()
351 hk_lower_multiview(nir_shader *nir) in hk_lower_multiview()
384 hk_nir_insert_psiz_write(nir_shader *nir) in hk_nir_insert_psiz_write()
489 agx_nir_lower_custom_border(nir_shader *nir) in agx_nir_lower_custom_border()
538 hk_lower_nir(struct hk_device *dev, nir_shader *nir, in hk_lower_nir()
725 nir_shader *nir, VkShaderCreateFlagsEXT shader_flags, in hk_compile_nir()
914 hk_lower_hw_vs(nir_shader *nir, struct hk_shader *shader) in hk_lower_hw_vs()
944 nir_shader *nir = info->nir; in hk_compile_shader() local
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/freedreno/ir3/ |
| H A D | ir3_cmdline.c | 63 sort_varyings(nir_shader *nir, nir_variable_mode mode) in sort_varyings()
75 fixup_varying_slots(nir_shader *nir, nir_variable_mode mode) in fixup_varying_slots()
106 nir_shader *nir = glsl_to_nir(&local_ctx.Const, in load_glsl() local
242 nir_shader *nir; in load_spirv() local
367 nir_shader *nir; in main() local
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/crocus/ |
| H A D | crocus_program.c | 220 crocus_lower_swizzles(struct nir_shader *nir, in crocus_lower_swizzles()
281 crocus_lower_storage_image_derefs(nir_shader *nir) in crocus_lower_storage_image_derefs()
326 crocus_fix_edge_flags(nir_shader *nir) in crocus_fix_edge_flags()
430 nir_shader *nir, in crocus_setup_uniforms()
820 struct nir_shader *nir, in crocus_setup_binding_table()
1138 crocus_lower_default_edgeflags(struct nir_shader *nir) in crocus_lower_default_edgeflags()
1171 nir_shader *nir = nir_shader_clone(mem_ctx, ish->nir); in crocus_compile_vs() local
1341 const nir_shader *nir = ish->nir; in crocus_get_shader_info() local
1396 nir_shader *nir; in crocus_compile_tcs() local
1530 nir_shader *nir = nir_shader_clone(mem_ctx, ish->nir); in crocus_compile_tes() local
[all …]
|
| /aosp_15_r20/external/mesa3d/src/gallium/frontends/rusticl/mesa/compiler/ |
| H A D | nir.rs | 143 nir: NonNull<nir_shader>, field
341 let nir = self.nir.as_ptr(); in set_workgroup_size_variable_if_zero() localVariable
350 let nir = unsafe { self.nir.as_mut() }; localVariable
383 let nir = self.nir.as_ptr(); in extract_constant_initializers() localVariable
411 let nir = unsafe { self.nir.as_mut() }; in take_printf_info() localVariable
441 let nir = self.nir.as_ref(); in get_constant_buffer() localVariable
468 let nir = unsafe { self.nir.as_ref() }; in reads_sysval() localVariable
|