From 3712cd27671e1acd10dd53a19bd225f276514de6 Mon Sep 17 00:00:00 2001 From: Rhys Perry Date: Wed, 8 Dec 2021 12:31:21 +0000 Subject: [PATCH] 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 Reviewed-by: Bas Nieuwenhuizen Part-of: --- src/amd/vulkan/radv_pipeline_rt.c | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/src/amd/vulkan/radv_pipeline_rt.c b/src/amd/vulkan/radv_pipeline_rt.c index 64dbf456ff3..4cea3109655 100644 --- a/src/amd/vulkan/radv_pipeline_rt.c +++ b/src/amd/vulkan/radv_pipeline_rt.c @@ -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);