| /third_party/mesa3d/src/intel/compiler/ |
| D | brw_gfx_ver_enum.h | 37 GFX8 = (1 << 6), enumerator
60 case 80: return GFX8; in gfx_ver_from_devinfo()
|
| D | brw_eu.c | 620 { BRW_OPCODE_SMOV, 10, "smov", 0, 0, GFX_GE(GFX8) & GFX_LT(GFX12) },
632 { BRW_OPCODE_CSEL, 18, "csel", 3, 1, GFX_GE(GFX8) & GFX_LT(GFX12) },
664 { BRW_OPCODE_GOTO, 46, "goto", 0, 0, GFX_GE(GFX8) },
702 { BRW_OPCODE_MADM, 93, "madm", 3, 1, GFX_GE(GFX8) },
|
| /third_party/mesa3d/src/amd/compiler/tests/ |
| D | test_isel.cpp | 62 for (unsigned i = GFX7; i <= GFX8; i++) {
85 for (unsigned i = GFX8; i <= GFX10; i++) {
114 for (unsigned i = GFX8; i <= GFX10; i++) {
|
| D | test_sdwa.cpp | 30 for (unsigned i = GFX8; i <= GFX10; i++) {
67 for (unsigned i = GFX8; i <= GFX10; i++) {
96 for (unsigned i = GFX8; i <= GFX10; i++) {
117 for (unsigned i = GFX8; i <= GFX10; i++) {
133 for (unsigned i = GFX8; i <= GFX10; i++) {
278 for (unsigned i = GFX8; i <= GFX10; i++) {
335 for (unsigned i = GFX8; i <= GFX10; i++) {
379 for (unsigned i = GFX8; i <= GFX10; i++) {
522 for (unsigned i = GFX8; i <= GFX9; i++) {
|
| D | test_builder.cpp | 29 for (unsigned i = GFX8; i <= GFX10; i++) {
|
| D | test_to_hw_instr.cpp | 226 for (amd_gfx_level lvl : {GFX8, GFX9, GFX11}) {
604 for (amd_gfx_level lvl : {GFX7, GFX8, GFX9, GFX11}) {
703 for (amd_gfx_level lvl : {GFX7, GFX8, GFX9, GFX11}) {
|
| /third_party/mesa3d/src/gallium/drivers/radeonsi/ |
| D | si_state_draw.cpp | 38 #define GFX(name) name##GFX8
139 if (!HAS_GS || GFX_VERSION <= GFX8) { in si_update_shaders()
146 assert(GFX_VERSION <= GFX8); in si_update_shaders()
161 if (GFX_VERSION <= GFX8) { in si_update_shaders()
188 if (GFX_VERSION <= GFX8) { in si_update_shaders()
196 if ((!HAS_TESS && !HAS_GS) || GFX_VERSION <= GFX8) { in si_update_shaders()
325 if ((GFX_VERSION <= GFX8 && in si_update_shaders()
332 if (GFX_VERSION <= GFX8) /* LS */ in si_update_shaders()
338 if (GFX_VERSION <= GFX8) /* ES */ in si_update_shaders()
346 if (GFX_VERSION <= GFX8) /* ES */ in si_update_shaders()
[all …]
|
| D | si_gpu_load.c | 104 if (sscreen->info.gfx_level == GFX7 || sscreen->info.gfx_level == GFX8) { in si_update_mmio_counters()
112 if (sscreen->info.gfx_level >= GFX8) { in si_update_mmio_counters()
|
| D | si_get.c | 238 if (sscreen->info.gfx_level <= GFX8) in si_get_param()
307 return sscreen->info.gfx_level <= GFX8 ? PIPE_QUIRK_TEXTURE_BORDER_COLOR_SWIZZLE_R600 : 0; in si_get_param()
501 return sscreen->info.gfx_level >= GFX8 && sscreen->options.fp16; in si_get_shader_param()
1116 .support_16bit_alu = sscreen->info.gfx_level >= GFX8, in si_init_screen_get_functions()
|
| D | si_shader_llvm_gs.c | 263 if (ctx->screen->info.gfx_level <= GFX8) { in si_preload_esgs_ring()
281 if (ctx->screen->info.gfx_level == GFX8) { in si_preload_esgs_ring()
367 unsigned data_format = ctx->ac.gfx_level == GFX8 || ctx->ac.gfx_level == GFX9 ? in si_preload_gs_rings()
|
| D | si_state.c | 106 if (sctx->gfx_level >= GFX8) { in si_emit_cb_render_state()
604 if (sctx->gfx_level >= GFX8 && sctx->gfx_level <= GFX10) in si_create_blend_state_mode()
615 if (sctx->gfx_level >= GFX8 && sctx->gfx_level <= GFX10 && logicop_enable) in si_create_blend_state_mode()
1843 if (sscreen->info.gfx_level <= GFX8) in si_translate_texformat()
2638 } else if (sctx->gfx_level >= GFX8) { in si_initialize_color_surface()
3438 sctx->gfx_level >= GFX8 ? 14 : 13); in si_emit_framebuffer_state()
3453 if (sctx->gfx_level >= GFX8) /* R_028C94_CB_COLOR0_DCC_BASE */ in si_emit_framebuffer_state()
3937 if (screen->info.gfx_level == GFX8) in si_make_buffer_descriptor()
4226 if (screen->info.gfx_level <= GFX8) in si_make_texture_descriptor()
4316 (screen->info.gfx_level <= GFX8 && res->target == PIPE_TEXTURE_3D))) { in si_make_texture_descriptor()
[all …]
|
| D | si_texture.c | 207 if (sscreen->info.gfx_level == GFX8) in si_init_surface()
218 if (sscreen->info.gfx_level >= GFX8 && modifier == DRM_FORMAT_MOD_INVALID && !is_imported) { in si_init_surface()
240 case GFX8: in si_init_surface()
560 if (sscreen->info.gfx_level <= GFX8) in si_displayable_dcc_needs_explicit_flush()
958 tex->tc_compatible_htile = (sscreen->info.gfx_level == GFX8 && in si_texture_create_object()
961 (sscreen->info.gfx_level >= GFX8 && in si_texture_create_object()
1008 if (sscreen->info.gfx_level == GFX8 && in si_texture_create_object()
1195 if (sscreen->info.gfx_level == GFX8 && tc_compatible_htile) in si_choose_tiling()
1263 sscreen->info.gfx_level >= GFX8 && in si_texture_create_with_modifier()
|
| /third_party/mesa3d/src/amd/compiler/ |
| D | aco_assembler.cpp | 308 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) { in emit_instruction()
331 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) { in emit_instruction()
353 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) { in emit_instruction()
389 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) { in emit_instruction()
425 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) { in emit_instruction()
516 } else if (ctx.gfx_level <= GFX8 || instr->isFlat()) { in emit_instruction()
566 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) { in emit_instruction()
597 if (ctx.gfx_level == GFX8 || ctx.gfx_level == GFX9) in emit_instruction()
675 assert(ctx.gfx_level >= GFX8); in emit_instruction()
711 assert(ctx.gfx_level >= GFX8 && ctx.gfx_level < GFX11); in emit_instruction()
|
| D | aco_ir.cpp | 80 case GFX8: program->family = CHIP_POLARIS10; break; in init_program()
112 } else if (program->gfx_level >= GFX8) { in init_program()
161 } else if (program->gfx_level >= GFX10 || program->gfx_level == GFX8) { in init_program()
208 if (gfx_level < GFX8 || gfx_level >= GFX11 || instr->isDPP() || instr->isVOP3P()) in can_use_SDWA()
218 if (vop3.clamp && instr->isVOPC() && gfx_level != GFX8) in can_use_SDWA()
252 if (gfx_level != GFX8 && is_mac) in can_use_SDWA()
256 if (!pre_ra && instr->isVOPC() && gfx_level == GFX8) in can_use_SDWA()
302 if (instr->definitions[0].getTemp().type() == RegType::sgpr && gfx_level == GFX8) in convert_to_SDWA()
|
| D | aco_print_asm.cpp | 122 case GFX8: in to_clrx_device_name()
417 if (program->gfx_level >= GFX8) { in check_print_asm_support()
448 if (program->gfx_level >= GFX8) { in print_asm()
|
| D | aco_validate.cpp | 156 check(program->gfx_level >= GFX8, "SDWA is GFX8 to GFX10.3 only", instr.get()); in validate_ir()
163 check(sdwa.clamp == false || program->gfx_level == GFX8, in validate_ir()
219 program->gfx_level == GFX8 && in validate_ir()
796 if (instr->isPseudo() && gfx_level >= GFX8) in validate_subdword_operand()
856 if (instr->isPseudo() && gfx_level >= GFX8) in validate_subdword_definition()
891 return gfx_level >= GFX8 ? def.bytes() : def.size() * 4u; in get_subdword_bytes_written()
|
| D | aco_lower_to_hw_instr.cpp | 82 } else if (gfx_level >= GFX8) { in get_reduce_opcode()
92 } else if (gfx_level >= GFX8) { in get_reduce_opcode()
104 } else if (gfx_level >= GFX8) { in get_reduce_opcode()
114 } else if (gfx_level >= GFX8) { in get_reduce_opcode()
124 } else if (gfx_level >= GFX8) { in get_reduce_opcode()
134 } else if (gfx_level >= GFX8) { in get_reduce_opcode()
514 if (ctx->program->gfx_level >= GFX8 && ctx->program->gfx_level < GFX11) { in emit_reduction()
672 } else if (ctx->program->gfx_level >= GFX8) { in emit_reduction()
1067 if (op.bytes() == 4 && op.constantEquals(0x3e22f983) && ctx->program->gfx_level >= GFX8) in copy_constant()
1237 } else if (def.regClass().is_subdword() && ctx->program->gfx_level < GFX8) { in do_copy()
[all …]
|
| /third_party/mesa3d/src/amd/vulkan/winsys/null/ |
| D | radv_null_winsys.c | 98 info->gfx_level = GFX8; in radv_null_winsys_query_info()
125 else if (info->gfx_level >= GFX8) in radv_null_winsys_query_info()
|
| /third_party/mesa3d/src/amd/vulkan/ |
| D | si_cmd_buffer.c | 143 assert(device->physical_device->rad_info.gfx_level == GFX8); in si_emit_compute()
213 if (physical_device->rad_info.gfx_level <= GFX8) in si_emit_graphics()
221 if (physical_device->rad_info.gfx_level <= GFX8) { in si_emit_graphics()
512 } else if (physical_device->rad_info.gfx_level >= GFX8) { in si_emit_graphics()
595 assert(device->physical_device->rad_info.gfx_level == GFX8); in si_emit_graphics()
861 if (gfx_level <= GFX8 && info->max_se == 4 && multi_instances_smaller_than_primgroup) in si_get_ia_multi_vgt_param()
877 (gfx_level == GFX8 && in si_get_ia_multi_vgt_param()
890 if (gfx_level <= GFX8 && ia_switch_on_eoi) in si_get_ia_multi_vgt_param()
990 if (gfx_level == GFX7 || gfx_level == GFX8) { in si_cs_emit_write_event_eop()
1256 if (gfx_level <= GFX8) { in si_cs_emit_cache_flush()
[all …]
|
| /third_party/mesa3d/src/amd/common/ |
| D | ac_shader_util.c | 110 S_028A40_ES_WRITE_OPTIMIZE(gfx_level <= GFX8) | S_028A40_GS_WRITE_OPTIMIZE(1) | in ac_vgt_gs_mode()
457 if (dim == ac_image_cube || (gfx_level <= GFX8 && dim == ac_image_3d)) in ac_get_image_dim()
764 if (gfx_level <= GFX8) in ac_compute_esgs_workgroup_size()
|
| D | ac_gpu_info.c | 858 info->gfx_level = GFX8; in ac_query_gpu_info()
1054 info->gfx_level >= GFX10 || (info->gfx_level >= GFX8 && info->max_se >= 2); in ac_query_gpu_info()
1070 info->gfx_level >= GFX8 && info->gfx_level <= GFX9 && info->max_se >= 2; in ac_query_gpu_info()
1084 info->gfx_level >= GFX9 || (info->gfx_level >= GFX8 && info->me_fw_feature >= 41); in ac_query_gpu_info()
1086 info->cpdma_prefetch_writes_memory = info->gfx_level <= GFX8; in ac_query_gpu_info()
1090 info->has_tc_compat_zrange_bug = info->gfx_level >= GFX8 && info->gfx_level <= GFX9; in ac_query_gpu_info()
1279 } else if (info->gfx_level >= GFX8) { in ac_query_gpu_info()
1938 case GFX8: in ac_get_hs_info()
1958 if (info->gfx_level >= GFX8) in ac_get_hs_info()
|
| D | amd_family.h | 150 GFX8, enumerator
|
| /third_party/mesa3d/docs/relnotes/ |
| D | 19.3.5.rst | 163 - ac/llvm: fix 16-bit fmed3 on GFX8 and older gens
164 - ac/llvm: flush denorms for nir_op_fmed3 on GFX8 and older gens
|
| D | 20.0.1.rst | 165 - ac/llvm: fix 16-bit fmed3 on GFX8 and older gens
166 - ac/llvm: flush denorms for nir_op_fmed3 on GFX8 and older gens
|
| /third_party/skia/third_party/externals/swiftshader/third_party/llvm-10.0/llvm/lib/Target/AMDGPU/ |
| D | GCNProcessors.td | 96 // GCN GFX8 (Volcanic Islands (VI)).
|