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

radeonsi: fill aco shader info for mono standalone vs

Browse source 
Reviewed-by: Marek Olšák <marek.olsak@amd.com>
Signed-off-by: Qiang Yu <yuq825@gmail.com>
Part-of: <https://gitlab.freedesktop.org/mesa/mesa/-/merge_requests/23096>
This commit is contained in:
Qiang Yu 2023-04-28 15:51:09 +08:00
parent 5351209632
commit 142485ff64
1 changed files with 11 additions and 0 deletions
Show stats Download patch file Download diff file Expand all files Collapse all files

11
src/gallium/drivers/radeonsi/si_shader_aco.c
View file

@ -60,6 +60,7 @@ static void
si_fill_aco_shader_info(struct si_shader *shader, struct aco_shader_info *info)
{
const struct si_shader_selector *sel = shader->selector;
const union si_shader_key *key = &shader->key;
info->wave_size = shader->wave_size;
info->workgroup_size = si_get_max_workgroup_size(shader);
@ -69,7 +70,17 @@ si_fill_aco_shader_info(struct si_shader *shader, struct aco_shader_info *info)
info->image_2d_view_of_3d = sel->screen->info.gfx_level == GFX9;
if (sel->stage <= MESA_SHADER_GEOMETRY && key->ge.as_ngg && !key->ge.as_es) {
info->is_ngg = true;
info->has_ngg_culling = key->ge.opt.ngg_culling;
info->has_ngg_early_prim_export = gfx10_ngg_export_prim_early(shader);
}
switch (sel->stage) {
case MESA_SHADER_VERTEX:
info->vs.as_es = key->ge.as_es;
info->vs.as_ls = key->ge.as_ls;
break;
case MESA_SHADER_FRAGMENT:
info->ps.num_interp = si_get_ps_num_interp(shader);
info->ps.spi_ps_input = shader->config.spi_ps_input_ena;