Searched refs:as_ngg (Results 1 – 14 of 14) sorted by relevance
56 return shader->key.as_ngg || si_is_multi_part_shader(shader); in si_is_merged_shader()203 return shader->key.as_ngg ? 128 : 0; in si_get_max_workgroup_size()390 else if (shader->key.as_es || shader->key.as_ngg || stage == MESA_SHADER_GEOMETRY) in si_init_shader_args()513 if (ctx->shader->key.as_ngg) in si_init_shader_args()789 (sel->info.stage == MESA_SHADER_GEOMETRY || shader->key.as_ngg)) { in si_shader_binary_open()796 if (shader->key.as_ngg && sel->info.stage == MESA_SHADER_GEOMETRY) { in si_shader_binary_open()1067 else if (shader->key.as_ngg) in si_get_shader_name()1076 else if (shader->key.as_ngg) in si_get_shader_name()1176 fprintf(f, " as_ngg = %u\n", key->as_ngg); in si_dump_shader_key()1193 fprintf(f, " as_ngg = %u\n", key->as_ngg); in si_dump_shader_key()[all …]
586 unsigned as_ngg : 1; member596 unsigned as_ngg : 1; member648 unsigned as_ngg : 1; /* whether it's the last GE stage and NGG is enabled, member934 if (key->as_es && key->as_ngg) in si_get_main_shader_part()938 if (key->as_ngg) in si_get_main_shader_part()
156 else if (ctx->shader->key.as_es || ctx->shader->key.as_ngg) in si_llvm_create_func()875 if (shader->key.as_ngg) { in si_llvm_translate_nir()895 if (ctx->stage != MESA_SHADER_GEOMETRY && (shader->key.as_ngg && !shader->key.as_es)) { in si_llvm_translate_nir()937 shader->key.as_ngg && !shader->key.as_es && !shader->key.opt.ngg_culling) { in si_llvm_translate_nir()952 if (ctx->stage == MESA_SHADER_GEOMETRY && shader->key.as_ngg) in si_llvm_translate_nir()963 (shader->key.as_ngg && !shader->key.as_es)) { in si_llvm_translate_nir()1000 } else if (ctx->stage == MESA_SHADER_GEOMETRY && !shader->key.as_ngg) { in si_llvm_translate_nir()1121 prolog_key.vs_prolog.as_ngg = 1; in si_llvm_compile_shader()1208 gs_prolog_key.gs_prolog.as_ngg = shader->key.as_ngg; in si_llvm_compile_shader()1217 shader_es.key.as_ngg = shader->key.as_ngg; in si_llvm_compile_shader()
111 if (ctx->shader->key.as_ngg) in si_set_es_return_value_for_gs()202 if (ctx->shader->key.as_ngg) { in emit_gs_epilogue()231 if (ctx->shader->key.as_ngg) { in si_llvm_emit_vertex()306 if (ctx->shader->key.as_ngg) { in si_llvm_emit_primitive()
1757 else if (shader->key.as_ngg) in si_shader_init_pm4_state()1768 else if (shader->key.as_ngg) in si_shader_init_pm4_state()1774 if (shader->key.as_ngg) in si_shader_init_pm4_state()2273 main_part->key.as_ngg = key->as_ngg; in si_check_missing_main_part()2469 shader1_key.as_ngg = key->as_ngg; /* for Wave32 vs Wave64 */ in si_shader_select_with_key()2677 shader->key.as_ngg = 1; in si_init_shader_selector_async()2680 si_get_ir_cache_key(sel, shader->key.as_ngg, shader->key.as_es, ir_sha1_cache_key); in si_init_shader_selector_async()3445 } else if (shader->key.as_ngg) { in si_delete_shader()3458 } else if (shader->key.as_ngg) { in si_delete_shader()3814 else if (sctx->shader.vs.current->key.as_ngg) in si_update_scratch_relocs()[all …]
2034 sctx->shader.vs.key.as_ngg = 0; in si_shader_change_notify()2038 sctx->shader.tes.key.as_ngg = sctx->ngg; in si_shader_change_notify()2039 sctx->shader.gs.key.as_ngg = sctx->ngg; in si_shader_change_notify()2042 sctx->shader.tes.key.as_ngg = sctx->ngg; in si_shader_change_notify()2047 sctx->shader.vs.key.as_ngg = sctx->ngg; in si_shader_change_notify()2048 sctx->shader.gs.key.as_ngg = sctx->ngg; in si_shader_change_notify()2052 sctx->shader.vs.key.as_ngg = sctx->ngg; in si_shader_change_notify()
939 else if (key->as_ngg) in si_sqtt_pipe_to_rgp_shader_stage()948 else if (key->as_ngg) in si_sqtt_pipe_to_rgp_shader_stage()
633 bool pos_writes_edgeflag = shader->selector->info.writes_edgeflag && !shader->key.as_ngg; in si_llvm_build_vs_exports()999 else if (shader->key.as_ngg) in si_llvm_init_vs_callbacks()
118 assert(shader->key.as_ngg && !shader->key.as_es); in gfx10_ngg_export_prim_early()827 assert(shader->key.as_ngg); in gfx10_emit_ngg_culling_epilogue()
1973 shader->key.as_ngg, in si_get_shader_wave_size()
1091 else if (ctx->shader->key.as_ngg) in si_llvm_init_tes_callbacks()
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