From: Bas Nieuwenhuizen <bas@basnieuwenhuizen.nl>
Date: Sat, 21 Oct 2017 01:07:43 +0000 (+0200)
Subject: ac/nir: Set larged wrokgroup size for GS on GFX9.
X-Git-Url: https://git.libre-soc.org/?a=commitdiff_plain;h=24fe4e6143aa06a8aaa1b2cabaee84064a0efbd9;p=mesa.git

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 <airlied@redhat.com>
---

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: