From 24fe4e6143aa06a8aaa1b2cabaee84064a0efbd9 Mon Sep 17 00:00:00 2001 From: Bas Nieuwenhuizen Date: Sat, 21 Oct 2017 03:07:43 +0200 Subject: ac/nir: Set larged wrokgroup size for GS on GFX9. They don't take a single wave anymore and we need the barriers. Fixes: 6bc42855f92 'radv: enable GS on GFX9' Reviewed-by: Dave Airlie --- src/amd/common/ac_nir_to_llvm.c | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) (limited to 'src/amd') diff --git a/src/amd/common/ac_nir_to_llvm.c b/src/amd/common/ac_nir_to_llvm.c index 02420f46966..ca856bb2f9e 100644 --- a/src/amd/common/ac_nir_to_llvm.c +++ b/src/amd/common/ac_nir_to_llvm.c @@ -6457,7 +6457,7 @@ ac_nir_get_max_workgroup_size(enum chip_class chip_class, case MESA_SHADER_TESS_CTRL: return chip_class >= CIK ? 128 : 64; case MESA_SHADER_GEOMETRY: - return 64; + return chip_class >= GFX9 ? 128 : 64; case MESA_SHADER_COMPUTE: break; default: -- cgit v1.2.3