Home
last modified time | relevance | path

Searched refs:as_ngg (Results 1 - 9 of 9) sorted by relevance

/third_party/mesa3d/src/gallium/drivers/radeonsi/
H A Dsi_shader_llvm.c156 else if (ctx->shader->key.ge.as_es || ctx->shader->key.ge.as_ngg) in si_llvm_create_func()
191 if (ctx->stage <= MESA_SHADER_GEOMETRY && ctx->shader->key.ge.as_ngg && in si_llvm_create_func()
845 if (!ctx->shader->key.ge.as_ngg) in si_llvm_translate_nir()
851 if (shader->key.ge.as_ngg) { in si_llvm_translate_nir()
930 shader->key.ge.as_ngg && !shader->key.ge.as_es) { in si_llvm_translate_nir()
971 shader->key.ge.as_ngg && !shader->key.ge.as_es && !shader->key.ge.opt.ngg_culling) { in si_llvm_translate_nir()
986 if (ctx->stage == MESA_SHADER_GEOMETRY && shader->key.ge.as_ngg) in si_llvm_translate_nir()
999 (shader->key.ge.as_ngg && !shader->key.ge.as_es)) { in si_llvm_translate_nir()
1043 } else if (ctx->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) { in si_llvm_translate_nir()
1082 else if (shader->key.ge.as_ngg) in si_llvm_translate_nir()
[all...]
H A Dsi_shader.c76 return shader->key.ge.as_ngg || si_is_multi_part_shader(shader); in si_is_merged_shader()
230 return shader->key.ge.as_ngg ? 128 : 0; in si_get_max_workgroup_size()
412 else if (shader->key.ge.as_es || shader->key.ge.as_ngg || stage == MESA_SHADER_GEOMETRY) in si_init_shader_args()
552 if (ctx->shader->key.ge.as_ngg) in si_init_shader_args()
847 (sel->stage <= MESA_SHADER_GEOMETRY && shader->key.ge.as_ngg))) { in si_shader_binary_open()
854 if (sel->stage == MESA_SHADER_GEOMETRY && shader->key.ge.as_ngg) { in si_shader_binary_open()
1138 else if (shader->key.ge.as_ngg) in si_get_shader_name()
1147 else if (shader->key.ge.as_ngg) in si_get_shader_name()
1245 fprintf(f, " as_ngg = %u\n", key->ge.as_ngg); in si_dump_shader_key()
[all...]
H A Dsi_shader.h508 struct si_shader *main_shader_part_ngg; /* as_ngg is set in the key */
619 unsigned as_ngg : 1; member
679 unsigned as_ngg : 1; /* whether it's the last GE stage and NGG is enabled, member
1018 if (key->ge.as_es && key->ge.as_ngg) in si_get_main_shader_part()
1022 if (key->ge.as_ngg) in si_get_main_shader_part()
H A Dsi_state_shaders.cpp50 if ((stage == MESA_SHADER_VERTEX && shader->key.ge.as_es && !shader->key.ge.as_ngg) || in si_determine_wave_size()
51 (stage == MESA_SHADER_TESS_EVAL && shader->key.ge.as_es && !shader->key.ge.as_ngg) || in si_determine_wave_size()
52 (stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg)) in si_determine_wave_size()
320 shader->selector->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) { in si_load_shader_binary()
370 if (shader->selector->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) { in si_shader_cache_insert_shader()
439 if (shader->selector->stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg) in si_shader_cache_load_shader()
2046 else if (shader->key.ge.as_ngg)
2057 else if (shader->key.ge.as_ngg)
2063 if (shader->key.ge.as_ngg) {
2589 main_part->key.ge.as_ngg
[all...]
H A Dsi_shader_llvm_gs.c56 if (ctx->shader->key.ge.as_ngg) in si_set_es_return_value_for_gs()
171 if (ctx->shader->key.ge.as_ngg) { in si_llvm_emit_vertex()
249 if (ctx->shader->key.ge.as_ngg) { in si_llvm_emit_primitive()
H A Dsi_descriptors.c2127 * as_ngg = NGG enabled for the last geometry stage. in si_shader_change_notify()
2128 * If GS sets as_ngg, the previous stage must set as_ngg too. in si_shader_change_notify()
2133 sctx->shader.vs.key.ge.as_ngg = 0; in si_shader_change_notify()
2137 sctx->shader.tes.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()
2138 sctx->shader.gs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()
2141 sctx->shader.tes.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()
2146 sctx->shader.vs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()
2147 sctx->shader.gs.key.ge.as_ngg = sctx->ngg; in si_shader_change_notify()
2151 sctx->shader.vs.key.ge.as_ngg in si_shader_change_notify()
[all...]
H A Dsi_sqtt.c987 else if (key->ge.as_ngg) in si_sqtt_pipe_to_rgp_shader_stage()
996 else if (key->ge.as_ngg) in si_sqtt_pipe_to_rgp_shader_stage()
H A Dsi_shader_llvm_vs.c574 bool pos_writes_edgeflag = shader->selector->info.writes_edgeflag && !shader->key.ge.as_ngg; in si_llvm_build_vs_exports()
H A Dgfx10_shader_ngg.c130 assert(shader->key.ge.as_ngg && !shader->key.ge.as_es); in gfx10_ngg_export_prim_early()
1020 assert(shader->key.ge.as_ngg); in gfx10_ngg_culling_build_end()

Completed in 22 milliseconds