radv: use 8x4 workgroups for wave32 RT

Beginning of Quake II RTX, 50% resolution scale, RX 6800: 54 -> 56 FPS.

Signed-off-by: Rhys Perry <pendingchaos02@gmail.com>
Reviewed-by: Bas Nieuwenhuizen <bas@basnieuwenhuizen.nl>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/14011>
This commit is contained in:
Rhys Perry 2021-12-08 12:31:21 +00:00 committed by Marge Bot
parent e7002b6f96
commit 3712cd2767

View file

@ -2091,7 +2091,7 @@ create_rt_shader(struct radv_device *device, const VkRayTracingPipelineCreateInf
nir_builder b = nir_builder_init_simple_shader(MESA_SHADER_COMPUTE, NULL, "rt_combined");
b.shader->info.workgroup_size[0] = 8;
b.shader->info.workgroup_size[1] = 8;
b.shader->info.workgroup_size[1] = device->physical_device->rt_wave_size == 64 ? 8 : 4;
b.shader->info.workgroup_size[2] = 1;
struct rt_variables vars = create_rt_variables(b.shader, stack_sizes);