| /aosp_15_r20/external/mesa3d/src/amd/compiler/ |
| H A D | aco_ir.cpp | 61 enum amd_gfx_level gfx_level, enum radeon_family family, bool wgp_mode, in init_program()
213 is_wait_export_ready(amd_gfx_level gfx_level, const Instruction* instr) in is_wait_export_ready()
248 can_use_SDWA(amd_gfx_level gfx_level, const aco_ptr<Instruction>& instr, bool pre_ra) in can_use_SDWA()
316 convert_to_SDWA(amd_gfx_level gfx_level, aco_ptr<Instruction>& instr) in convert_to_SDWA()
361 can_use_DPP(amd_gfx_level gfx_level, const aco_ptr<Instruction>& instr, bool dpp8) in can_use_DPP()
439 convert_to_DPP(amd_gfx_level gfx_level, aco_ptr<Instruction>& instr, bool dpp8) in convert_to_DPP()
505 can_use_input_modifiers(amd_gfx_level gfx_level, aco_opcode op, int idx) in can_use_input_modifiers()
518 can_use_opsel(amd_gfx_level gfx_level, aco_opcode op, int idx) in can_use_opsel()
596 instr_is_16bit(amd_gfx_level gfx_level, aco_opcode op) in instr_is_16bit()
1204 wait_imm::max(enum amd_gfx_level gfx_level) in max()
[all …]
|
| H A D | aco_print_ir.cpp | 246 print_cache_flags(enum amd_gfx_level gfx_level, const T& instr, FILE* output) in print_cache_flags()
318 print_instr_format_specific(enum amd_gfx_level gfx_level, const Instruction* instr, FILE* output) in print_instr_format_specific()
804 print_vopd_instr(enum amd_gfx_level gfx_level, const Instruction* instr, FILE* output, in print_vopd_instr()
907 aco_print_block(enum amd_gfx_level gfx_level, const Block* block, FILE* output, unsigned flags, in aco_print_block()
981 aco_print_instr(enum amd_gfx_level gfx_level, const Instruction* instr, FILE* output, in aco_print_instr()
|
| H A D | aco_scheduler.cpp | 112 amd_gfx_level gfx_level; member
411 is_done_sendmsg(amd_gfx_level gfx_level, const Instruction* instr) in is_done_sendmsg()
419 is_pos_prim_export(amd_gfx_level gfx_level, const Instruction* instr) in is_pos_prim_export()
455 amd_gfx_level gfx_level; member
479 add_memory_event(amd_gfx_level gfx_level, memory_event_set* set, Instruction* instr, in add_memory_event()
|
| H A D | aco_print_asm.cpp | 87 to_clrx_device_name(amd_gfx_level gfx_level, radeon_family family) in to_clrx_device_name()
253 disasm_instr(amd_gfx_level gfx_level, LLVMDisasmContextRef disasm, uint32_t* binary, in disasm_instr()
|
| H A D | aco_validate.cpp | 1165 validate_subdword_operand(amd_gfx_level gfx_level, const aco_ptr<Instruction>& instr, in validate_subdword_operand()
1228 validate_subdword_definition(amd_gfx_level gfx_level, const aco_ptr<Instruction>& instr) in validate_subdword_definition()
1266 amd_gfx_level gfx_level = program->gfx_level; in get_subdword_bytes_written() local
|
| /aosp_15_r20/external/mesa3d/src/amd/common/ |
| H A D | ac_shader_util.c | 135 enum amd_gfx_level gfx_level = *(enum amd_gfx_level *)data; in ac_nir_mem_vectorize_callback() local
253 uint32_t ac_vgt_gs_mode(unsigned gs_max_vert_out, enum amd_gfx_level gfx_level) in ac_vgt_gs_mode()
277 unsigned ac_get_tbuffer_format(enum amd_gfx_level gfx_level, unsigned dfmt, unsigned nfmt) in ac_get_tbuffer_format()
703 is_fetch_size_safe(const enum amd_gfx_level gfx_level, const struct ac_vtx_format_info* vtx_info, in is_fetch_size_safe()
719 ac_get_safe_fetch_size(const enum amd_gfx_level gfx_level, const struct ac_vtx_format_info* vtx_inf… in ac_get_safe_fetch_size()
752 enum ac_image_dim ac_get_sampler_dim(enum amd_gfx_level gfx_level, enum glsl_sampler_dim dim, in ac_get_sampler_dim()
779 enum ac_image_dim ac_get_image_dim(enum amd_gfx_level gfx_level, enum glsl_sampler_dim sdim, in ac_get_image_dim()
1074 unsigned ac_compute_lshs_workgroup_size(enum amd_gfx_level gfx_level, gl_shader_stage stage, in ac_compute_lshs_workgroup_size()
1097 unsigned ac_compute_esgs_workgroup_size(enum amd_gfx_level gfx_level, unsigned wave_size, in ac_compute_esgs_workgroup_size()
1327 union ac_hw_cache_flags ac_get_hw_cache_flags(enum amd_gfx_level gfx_level, in ac_get_hw_cache_flags()
[all …]
|
| H A D | ac_debug.c | 15 const struct si_reg *ac_find_register(enum amd_gfx_level gfx_level, enum radeon_family family, in ac_find_register()
82 const char *ac_get_register_name(enum amd_gfx_level gfx_level, enum radeon_family family, in ac_get_register_name()
90 bool ac_register_exists(enum amd_gfx_level gfx_level, enum radeon_family family, in ac_register_exists()
103 bool ac_vm_fault_occurred(enum amd_gfx_level gfx_level, uint64_t *old_dmesg_timestamp, in ac_vm_fault_occurred()
293 unsigned ac_get_wave_info(enum amd_gfx_level gfx_level, const struct radeon_info *info, in ac_get_wave_info()
427 void ac_print_gpuvm_fault_status(FILE *output, enum amd_gfx_level gfx_level, in ac_print_gpuvm_fault_status()
|
| H A D | ac_descriptors.c | 39 ac_build_sampler_descriptor(const enum amd_gfx_level gfx_level, const struct ac_sampler_state *stat… in ac_build_sampler_descriptor()
91 ac_build_gfx6_fmask_descriptor(const enum amd_gfx_level gfx_level, const struct ac_fmask_state *sta… in ac_build_gfx6_fmask_descriptor()
237 ac_build_gfx10_fmask_descriptor(const enum amd_gfx_level gfx_level, const struct ac_fmask_state *st… in ac_build_gfx10_fmask_descriptor()
317 ac_build_fmask_descriptor(const enum amd_gfx_level gfx_level, const struct ac_fmask_state *state, u… in ac_build_fmask_descriptor()
414 ac_get_gfx10_img_format(const enum amd_gfx_level gfx_level, const struct ac_texture_state *state) in ac_get_gfx10_img_format()
733 ac_set_buf_desc_word3(const enum amd_gfx_level gfx_level, const struct ac_buffer_state *state, uint… in ac_set_buf_desc_word3()
785 ac_build_buffer_descriptor(const enum amd_gfx_level gfx_level, const struct ac_buffer_state *state,… in ac_build_buffer_descriptor()
805 ac_build_raw_buffer_descriptor(const enum amd_gfx_level gfx_level, uint64_t va, uint32_t size, uint… in ac_build_raw_buffer_descriptor()
821 ac_build_attr_ring_descriptor(const enum amd_gfx_level gfx_level, uint64_t va, uint32_t size, uint3… in ac_build_attr_ring_descriptor()
|
| H A D | ac_nir_lower_resinfo.c | 27 enum amd_gfx_level gfx_level) in query_samples()
45 static nir_def *query_levels(nir_builder *b, nir_def *desc, enum amd_gfx_level gfx_level) in query_levels()
64 enum glsl_sampler_dim dim, bool is_array, enum amd_gfx_level gfx_level) in lower_query_size()
236 enum amd_gfx_level gfx_level = *(enum amd_gfx_level*)data; in lower_resinfo() local
369 bool ac_nir_lower_resinfo(nir_shader *nir, enum amd_gfx_level gfx_level) in ac_nir_lower_resinfo()
|
| H A D | ac_nir.c | 97 const enum amd_gfx_level gfx_level; member
182 ac_nir_lower_intrinsics_to_args(nir_shader *shader, const enum amd_gfx_level gfx_level, in ac_nir_lower_intrinsics_to_args()
364 enum amd_gfx_level gfx_level, in ac_nir_export_position()
647 enum amd_gfx_level gfx_level) in ac_nir_lower_indirect_derefs()
784 enum amd_gfx_level gfx_level, in ac_nir_create_gs_copy_shader()
931 enum amd_gfx_level gfx_level, in ac_nir_lower_legacy_vs()
1432 can_use_fmamix(nir_scalar s, enum amd_gfx_level gfx_level) in can_use_fmamix()
1461 enum amd_gfx_level gfx_level = *(enum amd_gfx_level *)param; in split_pack_half() local
1487 ac_nir_opt_pack_half(nir_shader *shader, enum amd_gfx_level gfx_level) in ac_nir_opt_pack_half()
|
| H A D | ac_formats.c | 448 ac_get_cb_format(enum amd_gfx_level gfx_level, enum pipe_format format) in ac_get_cb_format()
566 ac_translate_colorswap(enum amd_gfx_level gfx_level, enum pipe_format format, bool do_endian_swap) in ac_translate_colorswap()
630 ac_is_colorbuffer_format_supported(enum amd_gfx_level gfx_level, enum pipe_format format) in ac_is_colorbuffer_format_supported()
|
| H A D | ac_nir_lower_esgs_io_to_mem.c | 28 enum amd_gfx_level gfx_level; member
331 enum amd_gfx_level gfx_level, in ac_nir_lower_es_outputs_to_mem()
350 enum amd_gfx_level gfx_level, in ac_nir_lower_gs_inputs_to_mem()
|
| H A D | ac_nir.h | 121 enum amd_gfx_level gfx_level; member
254 enum amd_gfx_level gfx_level; member
289 enum amd_gfx_level gfx_level; member
|
| H A D | ac_shadowed_regs.c | 720 void ac_get_reg_ranges(enum amd_gfx_level gfx_level, enum radeon_family family, in ac_get_reg_ranges()
3518 static void ac_print_nonshadowed_reg(enum amd_gfx_level gfx_level, enum radeon_family family, in ac_print_nonshadowed_reg()
3547 void ac_print_nonshadowed_regs(enum amd_gfx_level gfx_level, enum radeon_family family) in ac_print_nonshadowed_regs()
|
| /aosp_15_r20/external/mesa3d/src/amd/vulkan/ |
| H A D | radv_shader_args.c | 84 declare_global_input_sgprs(const enum amd_gfx_level gfx_level, const struct radv_shader_info *info, in declare_global_input_sgprs()
149 declare_vs_input_vgprs(enum amd_gfx_level gfx_level, const struct radv_shader_info *info, struct ra… in declare_vs_input_vgprs()
317 radv_declare_rt_shader_args(enum amd_gfx_level gfx_level, struct radv_shader_args *args) in radv_declare_rt_shader_args()
392 declare_unmerged_vs_tcs_args(const enum amd_gfx_level gfx_level, const struct radv_shader_info *inf… in declare_unmerged_vs_tcs_args()
439 declare_unmerged_vs_tes_gs_args(const enum amd_gfx_level gfx_level, const struct radv_shader_info *… in declare_unmerged_vs_tes_gs_args()
521 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in declare_shader_args() local
884 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_declare_shader_args() local
|
| H A D | radv_cs.c | 19 radv_cs_emit_write_event_eop(struct radeon_cmdbuf *cs, enum amd_gfx_level gfx_level, enum radv_queu… in radv_cs_emit_write_event_eop()
134 gfx10_cs_emit_cache_flush(struct radeon_cmdbuf *cs, enum amd_gfx_level gfx_level, uint32_t *flush_c… in gfx10_cs_emit_cache_flush()
368 …_emit_cache_flush(struct radeon_winsys *ws, struct radeon_cmdbuf *cs, enum amd_gfx_level gfx_level, in radv_cs_emit_cache_flush()
571 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_emit_cond_exec() local
|
| H A D | radv_cp_dma.c | 35 cp_dma_max_byte_count(enum amd_gfx_level gfx_level) in cp_dma_max_byte_count()
136 enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_cs_cp_dma_prefetch() local
224 enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_cp_dma_buffer_copy() local
305 enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_cp_dma_clear_buffer() local
|
| H A D | radv_debug.c | 130 radv_dump_buffer_descriptor(enum amd_gfx_level gfx_level, enum radeon_family family, const uint32_t… in radv_dump_buffer_descriptor()
138 radv_dump_image_descriptor(enum amd_gfx_level gfx_level, enum radeon_family family, const uint32_t … in radv_dump_image_descriptor()
152 radv_dump_sampler_descriptor(enum amd_gfx_level gfx_level, enum radeon_family family, const uint32_… in radv_dump_sampler_descriptor()
161 radv_dump_combined_image_sampler_descriptor(enum amd_gfx_level gfx_level, enum radeon_family family, in radv_dump_combined_image_sampler_descriptor()
172 enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_dump_descriptor_set() local
502 enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_dump_queue_state() local
991 enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_dump_sq_hw_regs() local
|
| H A D | radv_spm.c | 50 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_emit_spm_counters() local
131 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_emit_spm_setup() local
|
| H A D | radv_shader_info.c | 1034 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_get_user_data_0() local
1091 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in radv_is_merged_shader_compiled_separately() local
1427 const enum amd_gfx_level gfx_level = pdev->info.gfx_level; in gfx10_get_ngg_info() local
1860 radv_select_hw_stage(const struct radv_shader_info *const info, const enum amd_gfx_level gfx_level) in radv_select_hw_stage()
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/radeonsi/ci/ |
| H A D | radeonsi-run-tests.py | 210 gfx_level = -1 variable
231 gfx_level = int(line.split("=")[1]) variable
344 def select_baseline(basepath, gfx_level, gpu_name): argument
|
| /aosp_15_r20/external/mesa3d/src/amd/registers/ |
| H A D | parse_kernel_headers.py | 89 def register_filter(gfx_level, name, offset, already_added): argument
816 def generate_json(gfx_level, amd_headers_path): argument
|
| /aosp_15_r20/external/mesa3d/src/amd/compiler/tests/ |
| H A D | helpers.cpp | 64 create_program(enum amd_gfx_level gfx_level, Stage stage, unsigned wave_size, in create_program()
92 setup_cs(const char* input_spec, enum amd_gfx_level gfx_level, enum radeon_family family, in setup_cs()
127 setup_nir_cs(enum amd_gfx_level gfx_level, gl_shader_stage stage, enum radeon_family family, const … in setup_nir_cs()
617 get_vk_device(enum amd_gfx_level gfx_level) in get_vk_device()
|
| /aosp_15_r20/external/mesa3d/src/gallium/drivers/r600/ |
| H A D | eg_debug.c | 125 int trace_id, enum amd_gfx_level gfx_level, in ac_parse_packet3()
267 const char *name, enum amd_gfx_level gfx_level, in eg_parse_ib()
|
| /aosp_15_r20/external/mesa3d/src/amd/vulkan/nir/ |
| H A D | radv_nir_lower_abi.c | 21 enum amd_gfx_level gfx_level; member
552 radv_nir_lower_abi(nir_shader *shader, enum amd_gfx_level gfx_level, const struct radv_shader_stage… in radv_nir_lower_abi()
|