Lines Matching refs:max_gsprims
2393 clamp_gsprims_to_esverts(unsigned *max_gsprims, unsigned max_esverts, unsigned min_verts_per_prim,
2399 *max_gsprims = MIN2(*max_gsprims, 1 + max_reuse);
2467 ngg->max_gsprims = 1;
2475 ac_compute_ngg_workgroup_size(ngg->hw_max_esverts, ngg->max_gsprims,
2574 unsigned max_gsprims = max_gsprims_base;
2580 max_gsprims = MIN2(max_gsprims, target_lds_size / gsprim_lds_size);
2582 max_esverts = MIN2(max_esverts, max_gsprims * max_verts_per_prim);
2583 clamp_gsprims_to_esverts(&max_gsprims, max_esverts, min_verts_per_prim, uses_adjacency);
2584 assert(max_esverts >= max_verts_per_prim && max_gsprims >= 1);
2594 unsigned lds_total = max_esverts * esvert_lds_size + max_gsprims * gsprim_lds_size;
2597 max_gsprims = max_gsprims * target_lds_size / lds_total;
2599 max_esverts = MIN2(max_esverts, max_gsprims * max_verts_per_prim);
2600 clamp_gsprims_to_esverts(&max_gsprims, max_esverts, min_verts_per_prim, uses_adjacency);
2601 assert(max_esverts >= max_verts_per_prim && max_gsprims >= 1);
2620 orig_max_gsprims = max_gsprims;
2626 MIN2(max_esverts, (max_lds_size - max_gsprims * gsprim_lds_size) / esvert_lds_size);
2627 max_esverts = MIN2(max_esverts, max_gsprims * max_verts_per_prim);
2635 max_gsprims = align(max_gsprims, wavesize);
2636 max_gsprims = MIN2(max_gsprims, max_gsprims_base);
2641 * workgroup, which is e.g. max_gsprims * 3
2644 unsigned usable_esverts = MIN2(max_esverts, max_gsprims * max_verts_per_prim);
2645 max_gsprims = MIN2(max_gsprims,
2648 clamp_gsprims_to_esverts(&max_gsprims, max_esverts, min_verts_per_prim, uses_adjacency);
2649 assert(max_esverts >= max_verts_per_prim && max_gsprims >= 1);
2650 } while (orig_max_esverts != max_esverts || orig_max_gsprims != max_gsprims);
2667 ? max_gsprims * gs_num_invocations * gs_info->gs.vertices_out
2688 ngg->max_gsprims = max_gsprims;
2692 ngg->ngg_emit_size = max_gsprims * gsprim_lds_size;
2696 ngg->esgs_ring_size = MIN2(max_esverts, max_gsprims * max_verts_per_prim) * esvert_lds_size * 4;
2709 max_esverts, max_gsprims * gs_num_invocations, max_out_vertices, prim_amp_factor);
3445 unsigned max_vtx_in = MIN2(256, ngg_info->enable_vertex_grouping ? ngg_info->hw_max_esverts : num_vertices_per_prim * ngg_info->max_gsprims);
5849 S_028A44_GS_PRIMS_PER_SUBGRP(ngg_state->max_gsprims) |
5850 S_028A44_GS_INST_PRIMS_IN_SUBGRP(ngg_state->max_gsprims * gs_num_invocations));
5864 ge_cntl = S_03096C_PRIMS_PER_SUBGRP(ngg_state->max_gsprims) |
5871 ge_cntl = S_03096C_PRIM_GRP_SIZE_GFX10(ngg_state->max_gsprims) |