Searched refs:as_ngg (Results 1 – 14 of 14) sorted by relevance
65 return shader->key.ge.as_ngg || si_is_multi_part_shader(shader); in si_is_merged_shader()164 if (shader->key.ge.as_ngg) in si_get_max_workgroup_size()284 shader->key.ge.as_ngg ? NULL : &args->ac.vs_prim_id); in declare_vs_input_vgprs()358 else if (shader->key.ge.as_es || shader->key.ge.as_ngg || stage == MESA_SHADER_GEOMETRY) in si_init_shader_args()484 if (shader->key.ge.as_ngg) in si_init_shader_args()793 (sel->stage <= MESA_SHADER_GEOMETRY && shader->key.ge.as_ngg))) { in si_shader_binary_open()800 if (sel->stage == MESA_SHADER_GEOMETRY && shader->key.ge.as_ngg) { in si_shader_binary_open()1053 (stage == MESA_SHADER_GEOMETRY || shader->key.ge.as_ngg)) { in calculate_needed_lds_size()1056 if (stage == MESA_SHADER_GEOMETRY && shader->key.ge.as_ngg) in calculate_needed_lds_size()1059 if (shader->key.ge.as_ngg) { in calculate_needed_lds_size()[all …]
141 else if (ctx->shader->key.ge.as_es || ctx->shader->key.ge.as_ngg) in si_llvm_create_func()177 ctx->shader->key.ge.as_ngg && si_shader_uses_streamout(ctx->shader)) in si_llvm_create_func()573 if (ctx->shader->key.ge.as_ngg) { in si_llvm_translate_nir()613 shader->key.ge.as_ngg && !shader->key.ge.as_es; in si_llvm_translate_nir()662 shader->key.ge.as_ngg && !shader->key.ge.as_es && !shader->key.ge.opt.ngg_culling) in si_llvm_translate_nir()667 if ((ctx->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) || in si_llvm_translate_nir()774 if (!ctx->shader->key.ge.as_ngg) in si_llvm_translate_nir()
82 if (stage <= MESA_SHADER_GEOMETRY && key->ge.as_ngg && !key->ge.as_es) { in si_fill_aco_shader_info()215 assert(sel->stage <= MESA_SHADER_GEOMETRY && key->ge.as_ngg); in si_aco_resolve_symbols()222 assert(sel->stage == MESA_SHADER_GEOMETRY && key->ge.as_ngg); in si_aco_resolve_symbols()
687 unsigned as_ngg : 1; /* whether it's the last GE stage and NGG is enabled, member1053 if (key->ge.as_es && key->ge.as_ngg) in si_get_main_shader_part()1060 if (key->ge.as_ngg) in si_get_main_shader_part()
44 if ((stage == MESA_SHADER_VERTEX && shader->key.ge.as_es && !shader->key.ge.as_ngg) || in si_determine_wave_size()45 (stage == MESA_SHADER_TESS_EVAL && shader->key.ge.as_es && !shader->key.ge.as_ngg) || in si_determine_wave_size()46 (stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg)) in si_determine_wave_size()307 shader->selector->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) { in si_load_shader_binary()357 if (shader->selector->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) { in si_shader_cache_insert_shader()426 if (shader->selector->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) in si_shader_cache_load_shader()2238 else if (shader->key.ge.as_ngg) in si_shader_init_pm4_state()2249 else if (shader->key.ge.as_ngg) in si_shader_init_pm4_state()2255 if (shader->key.ge.as_ngg) { in si_shader_init_pm4_state()2895 main_part->key.ge.as_ngg = key->ge.as_ngg; in si_check_missing_main_part()[all …]
40 if (ctx->shader->key.ge.as_ngg) in si_llvm_es_build_end()
2110 sctx->shader.vs.key.ge.as_ngg = 0; in si_shader_change_notify()2114 sctx->shader.tes.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()2115 sctx->shader.gs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()2118 sctx->shader.tes.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()2123 sctx->shader.vs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()2124 sctx->shader.gs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()2128 sctx->shader.vs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()
708 else if (key->ge.as_ngg) in si_sqtt_pipe_to_rgp_shader_stage()717 else if (key->ge.as_ngg) in si_sqtt_pipe_to_rgp_shader_stage()
47 assert(shader->key.ge.as_ngg && !shader->key.ge.as_es); in gfx10_ngg_export_prim_early()
899 if (key->ge.as_ngg) in si_select_hw_stage()910 if (key->ge.as_ngg) in si_select_hw_stage()
181 } else if (sel->stage == MESA_SHADER_GEOMETRY && !key->ge.as_ngg) { in build_gsvs_ring_desc()
322 - radeonsi/gfx10: fix the legacy pipeline by storing as_ngg in the329 - radeonsi/gfx10: add as_ngg variant for VS as ES to select Wave32/64
2321 - radeonsi/gfx10: fix the legacy pipeline by storing as_ngg in the2328 - radeonsi/gfx10: add as_ngg variant for VS as ES to select Wave32/64
3885 - radv: stop using the shader keys for as_ls/as_es/as_ngg when possible3905 - radv: stop using vs_common_out.{as_es/as_ls/as_ngg*} shader keys