Searched refs:as_ngg (Results 1 – 16 of 16) sorted by relevance
56 return shader->key.as_ngg || si_is_multi_part_shader(shader); in si_is_merged_shader()197 return shader->key.as_ngg ? 128 : 0; in si_get_max_workgroup_size()386 else if (shader->key.as_es || shader->key.as_ngg || stage == MESA_SHADER_GEOMETRY) in si_create_function()500 if (ctx->shader->key.as_ngg) in si_create_function()808 (sel->info.stage == MESA_SHADER_GEOMETRY || shader->key.as_ngg)) { in si_shader_binary_open()818 if (shader->key.as_ngg && sel->info.stage == MESA_SHADER_GEOMETRY) { in si_shader_binary_open()1082 else if (shader->key.as_ngg) in si_get_shader_name()1091 else if (shader->key.as_ngg) in si_get_shader_name()1193 fprintf(f, " as_ngg = %u\n", key->as_ngg); in si_dump_shader_key()1219 fprintf(f, " as_ngg = %u\n", key->as_ngg); in si_dump_shader_key()[all …]
557 unsigned as_ngg : 1; member571 unsigned as_ngg : 1; member623 unsigned as_ngg : 1; /* VS, TES, or GS compiled as NGG primitive shader */ member869 if (key->as_es && key->as_ngg) in si_get_main_shader_part()873 if (key->as_ngg) in si_get_main_shader_part()
121 if (ctx->shader->key.as_ngg) in si_set_es_return_value_for_gs()215 if (ctx->shader->key.as_ngg) { in emit_gs_epilogue()245 if (ctx->shader->key.as_ngg) { in si_llvm_emit_vertex()320 if (ctx->shader->key.as_ngg) { in si_llvm_emit_primitive()
1700 else if (shader->key.as_ngg) in si_shader_init_pm4_state()1711 else if (shader->key.as_ngg) in si_shader_init_pm4_state()1717 if (shader->key.as_ngg) in si_shader_init_pm4_state()1858 key->as_ngg = stages_key.u.ngg; in si_shader_selector_key()1860 key->as_ngg = stages_key.u.ngg; in si_shader_selector_key()1894 key->as_ngg = stages_key.u.ngg; in si_shader_selector_key()1912 key->as_ngg = stages_key.u.ngg; in si_shader_selector_key()2138 main_part->key.as_ngg = key->as_ngg; in si_check_missing_main_part()2284 shader1_key.as_ngg = key->as_ngg; /* for Wave32 vs Wave64 */ in si_shader_select_with_key()2481 shader->key.as_ngg = 1; in si_init_shader_selector_async()[all …]
1671 if (sctx->gs_shader.cso && sctx->gs_shader.current && !sctx->gs_shader.current->key.as_ngg) in si_get_vs_state()1929 shader->key.as_ngg, in si_get_shader_wave_size()
607 bool pos_writes_edgeflag = shader->selector->info.writes_edgeflag && !shader->key.as_ngg; in si_llvm_build_vs_exports()1017 else if (shader->key.as_ngg) in si_llvm_init_vs_callbacks()
157 else if (ctx->shader->key.as_es || ctx->shader->key.as_ngg) in si_llvm_create_func()
1089 else if (ctx->shader->key.as_ngg) in si_llvm_init_tes_callbacks()
127 assert(shader->key.as_ngg && !shader->key.as_es); in gfx10_ngg_export_prim_early()754 assert(shader->key.as_ngg); in gfx10_emit_ngg_culling_epilogue()
98 (args->options->key.vs_common_out.as_ngg && in needs_view_index_sgpr()308 if (args->options->key.vs_common_out.as_ngg) { in declare_vs_input_vgprs()440 if (is_pre_gs_stage(stage) && args->options->key.vs_common_out.as_ngg) { in radv_declare_shader_args()594 if (args->options->key.vs_common_out.as_ngg) { in radv_declare_shader_args()623 if (args->options->key.vs_common_out.as_ngg) { in radv_declare_shader_args()
469 if (!key->vs_common_out.as_ls && key->vs_common_out.as_ngg) in gather_info_output_decl()674 info->is_ngg = key->vs_common_out.as_ngg; in radv_nir_shader_info_pass()684 info->is_ngg = key->vs_common_out.as_ngg; in radv_nir_shader_info_pass()
318 if (is_pre_gs_stage(stage) && ctx->args->options->key.vs_common_out.as_ngg) { in create_function()774 if (ctx->args->options->key.vs_common_out.as_ngg) { in visit_emit_vertex_with_counter()829 if (ctx->args->options->key.vs_common_out.as_ngg) { in visit_end_primitive()3549 if (ctx->args->options->key.vs_common_out.as_ngg) { in emit_gs_epilogue()3572 else if (ctx->args->options->key.vs_common_out.as_ngg) in handle_shader_outputs_post()3591 else if (ctx->args->options->key.vs_common_out.as_ngg) in handle_shader_outputs_post()3843 args->options->key.vs_common_out.as_ngg) { in ac_translate_nir_to_llvm()3860 bool is_ngg = is_pre_gs_stage(shaders[0]->info.stage) && args->options->key.vs_common_out.as_ngg; in ac_translate_nir_to_llvm()3908 if (args->options->key.vs_common_out.as_ngg) { in ac_translate_nir_to_llvm()3965 args->options->key.vs_common_out.as_ngg && in ac_translate_nir_to_llvm()[all …]
58 uint32_t as_ngg:1; member
2631 keys[MESA_SHADER_TESS_EVAL].vs_common_out.as_ngg = true; in radv_fill_shader_keys()2633 keys[MESA_SHADER_VERTEX].vs_common_out.as_ngg = true; in radv_fill_shader_keys()2645 keys[MESA_SHADER_TESS_EVAL].vs_common_out.as_ngg = false; in radv_fill_shader_keys()2660 keys[MESA_SHADER_TESS_EVAL].vs_common_out.as_ngg = false; in radv_fill_shader_keys()2662 keys[MESA_SHADER_VERTEX].vs_common_out.as_ngg = false; in radv_fill_shader_keys()2672 keys[MESA_SHADER_TESS_EVAL].vs_common_out.as_ngg) { in radv_fill_shader_keys()2675 keys[MESA_SHADER_VERTEX].vs_common_out.as_ngg) { in radv_fill_shader_keys()2702 if (stage == MESA_SHADER_GEOMETRY && !key->vs_common_out.as_ngg) in radv_get_wave_size()3280 keys[MESA_SHADER_VERTEX].vs_common_out.as_ngg) || in radv_create_shaders()3282 keys[MESA_SHADER_TESS_EVAL].vs_common_out.as_ngg)) { in radv_create_shaders()
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