From 3f6b5ea27a22d0978cd564b86ff103cb30f33593 Mon Sep 17 00:00:00 2001
From: Caio Oliveira <caio.oliveira@intel.com>
Date: Fri, 30 Aug 2024 11:32:57 -0700
Subject: [PATCH] intel/brw: Use linear walk when shader requires
 DERIVATIVE_GROUP_LINEAR

Reviewed-by: Kenneth Graunke <kenneth@whitecape.org>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/30955>
---
 src/intel/compiler/brw_nir_lower_cs_intrinsics.c | 1 +
 1 file changed, 1 insertion(+)

diff --git a/src/intel/compiler/brw_nir_lower_cs_intrinsics.c b/src/intel/compiler/brw_nir_lower_cs_intrinsics.c
index 2d33e13b473..8722a89cca0 100644
--- a/src/intel/compiler/brw_nir_lower_cs_intrinsics.c
+++ b/src/intel/compiler/brw_nir_lower_cs_intrinsics.c
@@ -362,6 +362,7 @@ brw_nir_lower_cs_intrinsics(nir_shader *nir,
 
       /* TODO: more heuristics about 1D/SLM access vs. 2D access */
       bool linear =
+         state.derivative_group == DERIVATIVE_GROUP_LINEAR ||
          BITSET_TEST(nir->info.system_values_read,
                      SYSTEM_VALUE_LOCAL_INVOCATION_INDEX) ||
          (nir->info.workgroup_size[1] == 1 &&