fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-05-06 13:48:06 +02:00
Code Issues Projects Releases Packages Wiki Activity Actions 1

radv: fix max_waves calculation for tesselation

Browse source 
Totals from 337 (0.42% of 79839) affected shaders: (Navi48)

MaxWaves: 8084 -> 4474 (-44.66%)
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/37577>
This commit is contained in:
Daniel Schürmann 2025-10-10 11:32:26 +02:00 • committed by Marge Bot
parent 216d14fb65
commit c35d53667e
1 changed files with 4 additions and 8 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

12
src/amd/vulkan/radv_shader.c
View file

@ -2749,16 +2749,12 @@ radv_get_max_waves(const struct radv_device *device, const struct ac_shader_conf
const uint8_t wave_size = info->wave_size;
mesa_shader_stage stage = info->stage;
unsigned max_simd_waves = gpu_info->max_waves_per_simd;
unsigned lds_per_workgroup = 0;
unsigned waves_per_workgroup = 1;
unsigned lds_per_workgroup = align(conf->lds_size * gpu_info->lds_encode_granularity,
gpu_info->lds_alloc_granularity);
unsigned waves_per_workgroup = DIV_ROUND_UP(info->workgroup_size, wave_size);
if (stage == MESA_SHADER_FRAGMENT) {
lds_per_workgroup = conf->lds_size * gpu_info->lds_encode_granularity + info->ps.num_inputs * 48;
lds_per_workgroup = align(lds_per_workgroup, gpu_info->lds_alloc_granularity);
} else if (stage == MESA_SHADER_COMPUTE || stage == MESA_SHADER_TASK) {
unsigned max_workgroup_size = info->workgroup_size;
lds_per_workgroup = align(conf->lds_size * gpu_info->lds_encode_granularity, gpu_info->lds_alloc_granularity);
waves_per_workgroup = DIV_ROUND_UP(max_workgroup_size, wave_size);
lds_per_workgroup += align(info->ps.num_inputs * 48, gpu_info->lds_alloc_granularity);
}
if (conf->num_sgprs && gfx_level < GFX10) {