radv: fix PS epilogs with RADV_PERFTEST=pswave32

This option is rarely or even never used but it was broken. While we
are at it, remove radv_ps_epilog_key::wave32 because the wave size
can only be changed globally for PS.

Signed-off-by: Samuel Pitoiset <samuel.pitoiset@gmail.com>
Reviewed-by: Rhys Perry <pendingchaos02@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/20199>
This commit is contained in:
Samuel Pitoiset 2022-12-08 13:55:09 +01:00 committed by Marge Bot
parent b7f49de625
commit 67c9497435
2 changed files with 1 additions and 2 deletions

View file

@ -2643,7 +2643,7 @@ radv_create_ps_epilog(struct radv_device *device, const struct radv_ps_epilog_ke
device->instance->debug_flags & RADV_DEBUG_HANG, false);
struct radv_shader_info info = {0};
info.wave_size = key->wave32 ? 32 : 64;
info.wave_size = device->physical_device->ps_wave_size;
info.workgroup_size = 64;
radv_declare_ps_epilog_args(device->physical_device->rad_info.gfx_level, key, &args);

View file

@ -415,7 +415,6 @@ struct radv_ps_epilog_key {
uint8_t enable_mrt_output_nan_fixup;
bool mrt0_is_dual_src;
bool wave32;
};
enum radv_shader_binary_type { RADV_BINARY_TYPE_LEGACY, RADV_BINARY_TYPE_RTLD };