fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-05-07 02:48:06 +02:00
Code Issues Projects Releases Packages Wiki Activity Actions 4

brw: disable hw generate local ID for jay

Browse source 
Jay will need more work to handle these payloads properly especially in SIMD32.
For now just disable the optimization for Jay for correctness.

Signed-off-by: Alyssa Rosenzweig <alyssa.rosenzweig@intel.com>
Reviewed-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Reviewed-by: Kenneth Graunke <kenneth@whitecape.org>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/40835>
This commit is contained in:
Alyssa Rosenzweig 2026-02-26 17:19:22 -05:00 • committed by Marge Bot
parent e8b9f26561
commit 4778fc1ab7
1 changed files with 3 additions and 1 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

4
src/intel/compiler/brw/brw_nir_lower_cs_intrinsics.c
View file

@ -5,6 +5,7 @@
#include "brw_nir.h"
#include "compiler/nir/nir_builder.h"
#include "dev/intel_debug.h"
struct lower_intrinsics_state {
nir_shader *nir;
@ -323,7 +324,8 @@ brw_nir_lower_cs_intrinsics(nir_shader *nir,
nir->info.derivative_group != DERIVATIVE_GROUP_QUADS &&
!nir->info.workgroup_size_variable &&
util_is_power_of_two_nonzero(nir->info.workgroup_size[0]) &&
util_is_power_of_two_nonzero(nir->info.workgroup_size[1])) {
util_is_power_of_two_nonzero(nir->info.workgroup_size[1]) &&
!intel_use_jay(devinfo, nir->info.stage)) {
state.hw_generated_local_id = true;