fdo-mirrors/mesa
1
0
Fork 0
mirror of https://gitlab.freedesktop.org/mesa/mesa.git synced 2026-04-21 14:10:37 +02:00
Code Issues Projects Releases Packages Wiki Activity Actions 3

ac/nir: optimize mesh shader local_invocation_index

Browse source 
Signed-off-by: Rhys Perry <pendingchaos02@gmail.com>
Reviewed-by: Timur Kristóf <timur.kristof@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/25040>
This commit is contained in:
Rhys Perry 2023-09-07 17:01:14 +01:00 • committed by Marge Bot
parent cddbe9a4c2
commit c63ac28014
1 changed files with 13 additions and 0 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

13
src/amd/common/ac_nir_lower_ngg.c
View file

@ -4958,5 +4958,18 @@ ac_nir_lower_ngg_ms(nir_shader *shader,
nir_lower_alu_to_scalar(shader, NULL, NULL);
nir_lower_phis_to_scalar(shader, true);
/* Optimize load_local_invocation_index. When the API workgroup is smaller than the HW workgroup,
* local_invocation_id isn't initialized for all lanes and we can't perform this optimization for
* all load_local_invocation_index.
*/
if (fast_launch_2 && api_workgroup_size == hw_workgroup_size &&
((shader->info.workgroup_size[0] == 1) + (shader->info.workgroup_size[1] == 1) +
(shader->info.workgroup_size[2] == 1)) == 2) {
nir_lower_compute_system_values_options csv_options = {
.lower_local_invocation_index = true,
};
nir_lower_compute_system_values(shader, &csv_options);
}
nir_validate_shader(shader, "after emitting NGG MS");
}