fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2025-12-27 01:50:10 +01:00
Code Issues Projects Releases Packages Wiki Activity Actions 1

brw: remove driver specific load_num_workgroup lowering
Some checks are pending
macOS-CI / macOS-CI (dri) (push) Waiting to run
Details
macOS-CI / macOS-CI (xlib) (push) Waiting to run
Details

Browse source 
Signed-off-by: Lionel Landwerlin <lionel.g.landwerlin@intel.com>
Reviewed-by: Alyssa Rosenzweig <alyssa.rosenzweig@intel.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/38735>
This commit is contained in:
Lionel Landwerlin 2025-12-01 10:33:02 +02:00 • committed by Marge Bot
parent 578d2f0daa
commit 86419dd519
2 changed files with 0 additions and 24 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

1
src/intel/compiler/brw/brw_compiler.h
View file

@ -988,7 +988,6 @@ struct brw_cs_prog_data {
unsigned prog_spilled;
bool uses_barrier;
bool uses_num_work_groups;
bool uses_inline_data;
/** Whether inline push data is used to provide a 64bit pointer to push
* constants

23
src/intel/compiler/brw/brw_from_nir.cpp
View file

@ -4410,29 +4410,6 @@ brw_from_nir_emit_cs_intrinsic(nir_to_brw_state &ntb,
break;
}
case nir_intrinsic_load_num_workgroups: {
assert(instr->def.bit_size == 32);
cs_prog_data->uses_num_work_groups = true;
brw_reg srcs[MEMORY_LOGICAL_NUM_SRCS];
srcs[MEMORY_LOGICAL_BINDING] = brw_imm_ud(0);
srcs[MEMORY_LOGICAL_ADDRESS] = brw_imm_ud(0);
brw_mem_inst *mem =
bld.emit(SHADER_OPCODE_MEMORY_LOAD_LOGICAL,
dest, srcs, MEMORY_LOGICAL_NUM_SRCS)->as_mem();
mem->size_written = 3 * s.dispatch_width * 4;
mem->lsc_op = LSC_OP_LOAD;
mem->mode = MEMORY_MODE_UNTYPED;
mem->binding_type = LSC_ADDR_SURFTYPE_BTI;
mem->data_size = LSC_DATA_SIZE_D32;
mem->coord_components = 1;
mem->components = 3;
mem->alignment = 4;
break;
}
case nir_intrinsic_load_workgroup_size: {
/* Should have been lowered by brw_nir_lower_cs_intrinsics() or
* iris_setup_uniforms() for the variable group size case.