OpenHarmony/third_party_mesa3d
2
0
Fork 0
Code Issues Pull Requests Actions Packages Projects Releases Wiki Activity

intel/fs: Remove unused state from brw_nir_lower_cs_intrinsics

Browse Source 
After 2663759af0 ("intel/fs: Add and use a new load_simd_width_intel
intrinsic") the local_workgroup_size is not used anymore except for
assertions at the pass' start, so drop it from state struct.

Reviewed-by: Jason Ekstrand <jason@jlekstrand.net>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/5213>
This commit is contained in:
Caio Marcelo de Oliveira Filho
2020-05-20 02:37:49 -07:00
committed by Marge Bot
parent 5e0525e145
commit 2a308ee4c7
1 changed files with 11 additions and 16 deletions
Download Patch File Download Diff File Expand all files Collapse all files

23
src/intel/compiler/brw_nir_lower_cs_intrinsics.c
View File

@@ -29,7 +29,6 @@ struct lower_intrinsics_state {
nir_function_impl *impl; nir_function_impl *impl;
bool progress; bool progress;
nir_builder builder; nir_builder builder;
unsigned local_workgroup_size;
}; };
static bool static bool
@@ -203,22 +202,18 @@ brw_nir_lower_cs_intrinsics(nir_shader *nir)
.nir = nir, .nir = nir,
}; };
if (!nir->info.cs.local_size_variable) {
state.local_workgroup_size = nir->info.cs.local_size[0] *
nir->info.cs.local_size[1] *
nir->info.cs.local_size[2];
} else {
state.local_workgroup_size = nir->info.cs.max_variable_local_size;
}
/* Constraints from NV_compute_shader_derivatives. */ /* Constraints from NV_compute_shader_derivatives. */
if (nir->info.cs.derivative_group == DERIVATIVE_GROUP_QUADS && if (!nir->info.cs.local_size_variable) {
!nir->info.cs.local_size_variable) { if (nir->info.cs.derivative_group == DERIVATIVE_GROUP_QUADS) {
assert(nir->info.cs.local_size[0] % 2 == 0); assert(nir->info.cs.local_size[0] % 2 == 0);
assert(nir->info.cs.local_size[1] % 2 == 0); assert(nir->info.cs.local_size[1] % 2 == 0);
} else if (nir->info.cs.derivative_group == DERIVATIVE_GROUP_LINEAR && } else if (nir->info.cs.derivative_group == DERIVATIVE_GROUP_LINEAR) {
!nir->info.cs.local_size_variable) { ASSERTED unsigned local_workgroup_size =
assert(state.local_workgroup_size % 4 == 0); nir->info.cs.local_size[0] *
nir->info.cs.local_size[1] *
nir->info.cs.local_size[2];
assert(local_workgroup_size % 4 == 0);
}
} }
nir_foreach_function(function, nir) { nir_foreach_function(function, nir) {