From b8f2fb81f602f3d94c5a074f917b91f97d8555c6 Mon Sep 17 00:00:00 2001 From: =?UTF-8?q?Marek=20Ol=C5=A1=C3=A1k?= Date: Tue, 15 Apr 2025 23:11:57 -0400 Subject: [PATCH] ac/gpu_info: print tessellation ring info MIME-Version: 1.0 Content-Type: text/plain; charset=UTF-8 Content-Transfer-Encoding: 8bit Reviewed-by: Pierre-Eric Pelloux-Prayer Reviewed-by: Timur Kristóf Part-of: --- src/amd/common/ac_gpu_info.c | 20 ++++++++++++-------- 1 file changed, 12 insertions(+), 8 deletions(-) diff --git a/src/amd/common/ac_gpu_info.c b/src/amd/common/ac_gpu_info.c index 66b5d6c9fb4..05d4b94de22 100644 --- a/src/amd/common/ac_gpu_info.c +++ b/src/amd/common/ac_gpu_info.c @@ -2126,15 +2126,19 @@ void ac_print_gpu_info(const struct radeon_info *info, FILE *f) fprintf(f, " max_scratch_waves = %i\n", info->max_scratch_waves); fprintf(f, " has_scratch_base_registers = %i\n", info->has_scratch_base_registers); fprintf(f, "Ring info:\n"); - fprintf(f, " attribute_ring_size_per_se = %u KB\n", - DIV_ROUND_UP(info->attribute_ring_size_per_se, 1024)); - if (info->gfx_level >= GFX12) { - fprintf(f, " pos_ring_size_per_se = %u KB\n", DIV_ROUND_UP(info->pos_ring_size_per_se, 1024)); - fprintf(f, " prim_ring_size_per_se = %u KB\n", DIV_ROUND_UP(info->prim_ring_size_per_se, 1024)); + if (info->gfx_level >= GFX11) { + fprintf(f, " attribute_ring_size_per_se = %u KB\n", + DIV_ROUND_UP(info->attribute_ring_size_per_se, 1024)); + if (info->gfx_level >= GFX12) { + fprintf(f, " pos_ring_size_per_se = %u KB\n", DIV_ROUND_UP(info->pos_ring_size_per_se, 1024)); + fprintf(f, " prim_ring_size_per_se = %u KB\n", DIV_ROUND_UP(info->prim_ring_size_per_se, 1024)); + } + fprintf(f, " total_attribute_pos_prim_ring_size = %u KB\n", + DIV_ROUND_UP(info->total_attribute_pos_prim_ring_size, 1024)); } - fprintf(f, " total_attribute_pos_prim_ring_size = %u KB\n", - DIV_ROUND_UP(info->total_attribute_pos_prim_ring_size, 1024)); - + fprintf(f, " hs_offchip_workgroup_size = %u B\n", info->hs_offchip_workgroup_dw_size * 4); + fprintf(f, " tess_factor_ring_size = %u KB\n", DIV_ROUND_UP(info->tess_factor_ring_size, 1024)); + fprintf(f, " tess_offchip_ring_size = %u KB\n", DIV_ROUND_UP(info->tess_offchip_ring_size, 1024)); fprintf(f, "Render backend info:\n"); fprintf(f, " pa_sc_tile_steering_override = 0x%x\n", info->pa_sc_tile_steering_override); fprintf(f, " max_render_backends = %i\n", info->max_render_backends);