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

brw: add Jay-specific SIMD selection rule

Browse source 
In the future this might even do something clever.

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-04-07 14:20:45 -04:00 • committed by Marge Bot
parent f33454e35a
commit 3afd572d8f
1 changed files with 12 additions and 1 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

13
src/intel/compiler/brw/brw_shader.cpp
View file

@ -17,6 +17,7 @@
#include "dev/intel_wa.h"
#include "compiler/glsl_types.h"
#include "compiler/nir/nir_builder.h"
#include "util/bitscan.h"
#include "util/u_math.h"
void
@ -999,7 +1000,17 @@ brw_cs_get_dispatch_info(const struct intel_device_info *devinfo,
override_local_size ? override_local_size :
prog_data->local_size;
const int simd = brw_simd_select_for_workgroup_size(devinfo, prog_data, sizes);
int simd = -1;
if (intel_use_jay(devinfo, MESA_SHADER_COMPUTE)) {
/* Currently Jay compiles only a single binary, just select that. In the
* future this needs to get smarter.
*/
assert(util_is_power_of_two_nonzero(prog_data->prog_mask));
simd = util_logbase2(prog_data->prog_mask);
} else {
simd = brw_simd_select_for_workgroup_size(devinfo, prog_data, sizes);
}
assert(simd >= 0 && simd < 3);
info.group_size = sizes[0] * sizes[1] * sizes[2];