From ed2f496ce49f34f2fc2b3bf207b7fc439ca8d2b1 Mon Sep 17 00:00:00 2001 From: Andrey Konovalov Date: Thu, 3 Feb 2022 19:30:17 +0000 Subject: [PATCH] ir3: set local_size for shaders of MESA_SHADER_KERNEL type ir3_compile_shader_nir() should set local_size[] and local_size_variable fields not only for compute shaders, but for the OpenCL kernels too. v2: use gl_shader_stage_is_compute() instead of explicit comparison with MESA_SHADER_[COMPUTE,KERNEL]. Signed-off-by: Andrey Konovalov Part-of: --- src/freedreno/ir3/ir3_compiler_nir.c | 2 +- 1 file changed, 1 insertion(+), 1 deletion(-) diff --git a/src/freedreno/ir3/ir3_compiler_nir.c b/src/freedreno/ir3/ir3_compiler_nir.c index a3d09fdfe52..933ef90cba7 100644 --- a/src/freedreno/ir3/ir3_compiler_nir.c +++ b/src/freedreno/ir3/ir3_compiler_nir.c @@ -4618,7 +4618,7 @@ ir3_compile_shader_nir(struct ir3_compiler *compiler, ir = so->ir = ctx->ir; - if (so->type == MESA_SHADER_COMPUTE) { + if (gl_shader_stage_is_compute(so->type)) { so->local_size[0] = ctx->s->info.workgroup_size[0]; so->local_size[1] = ctx->s->info.workgroup_size[1]; so->local_size[2] = ctx->s->info.workgroup_size[2];