]>
Commit | Line | Data |
---|---|---|
3d8549dc JK |
1 | From 3b1a7e5333335900293935399ce49a67562eafc7 Mon Sep 17 00:00:00 2001 |
2 | From: Jason Ekstrand <jason@jlekstrand.net> | |
3 | Date: Tue, 3 Sep 2019 10:00:23 -0500 | |
4 | Subject: [PATCH] anv: Bump maxComputeWorkgroupSize | |
5 | ||
6 | Fixes: 9a129510f56f "anv: Bump maxComputeWorkgroupInvocations" | |
7 | Bugzilla: https://bugs.freedesktop.org/show_bug.cgi?id=111552 | |
8 | Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com> | |
9 | --- | |
10 | src/intel/vulkan/anv_device.c | 10 ++++++---- | |
11 | 1 file changed, 6 insertions(+), 4 deletions(-) | |
12 | ||
13 | diff --git a/src/intel/vulkan/anv_device.c b/src/intel/vulkan/anv_device.c | |
14 | index a6572135c91..3497a01f900 100644 | |
15 | --- a/src/intel/vulkan/anv_device.c | |
16 | +++ b/src/intel/vulkan/anv_device.c | |
17 | @@ -1264,6 +1264,8 @@ void anv_GetPhysicalDeviceProperties( | |
18 | pdevice->has_a64_buffer_access ? UINT32_MAX : | |
19 | MAX_BINDING_TABLE_SIZE - MAX_RTS; | |
20 | ||
21 | + const uint32_t max_workgroup_size = 32 * devinfo->max_cs_threads; | |
22 | + | |
23 | VkSampleCountFlags sample_counts = | |
24 | isl_device_get_sample_counts(&pdevice->isl_dev); | |
25 | ||
26 | @@ -1322,11 +1324,11 @@ void anv_GetPhysicalDeviceProperties( | |
27 | .maxFragmentCombinedOutputResources = 8, | |
28 | .maxComputeSharedMemorySize = 64 * 1024, | |
29 | .maxComputeWorkGroupCount = { 65535, 65535, 65535 }, | |
30 | - .maxComputeWorkGroupInvocations = 32 * devinfo->max_cs_threads, | |
31 | + .maxComputeWorkGroupInvocations = max_workgroup_size, | |
32 | .maxComputeWorkGroupSize = { | |
33 | - 16 * devinfo->max_cs_threads, | |
34 | - 16 * devinfo->max_cs_threads, | |
35 | - 16 * devinfo->max_cs_threads, | |
36 | + max_workgroup_size, | |
37 | + max_workgroup_size, | |
38 | + max_workgroup_size, | |
39 | }, | |
40 | .subPixelPrecisionBits = 8, | |
41 | .subTexelPrecisionBits = 8, | |
42 | -- | |
43 | 2.22.0 | |
44 |