Home
last modified time | relevance | path

Searched refs:MESA_SHADER_GEOMETRY (Results 1 - 25 of 166) sorted by relevance

1234567

/third_party/mesa3d/src/intel/common/
H A Dintel_urb_config.c112 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
134 [MESA_SHADER_GEOMETRY] = gs_present ? 2 : 0, in intel_get_urb_config()
145 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
150 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
163 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
197 chunks[MESA_SHADER_GEOMETRY] += remaining_space; in intel_get_urb_config()
202 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
210 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
247 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
/third_party/mesa3d/src/mesa/main/
H A Dshaderobj.h134 return MESA_SHADER_GEOMETRY; in _mesa_shader_enum_to_shader_stage()
154 case MESA_SHADER_GEOMETRY: in _mesa_shader_stage_to_subroutine_prefix()
176 return MESA_SHADER_GEOMETRY; in _mesa_shader_stage_from_subroutine_uniform()
196 return MESA_SHADER_GEOMETRY; in _mesa_shader_stage_from_subroutine()
216 case MESA_SHADER_GEOMETRY: in _mesa_shader_stage_to_subroutine()
237 case MESA_SHADER_GEOMETRY: in _mesa_shader_stage_to_subroutine_uniform()
H A Ddraw_validate.c294 if(shader->CurrentProgram[MESA_SHADER_GEOMETRY]) { in _mesa_update_valid_to_render_state()
295 switch (shader->CurrentProgram[MESA_SHADER_GEOMETRY]-> in _mesa_update_valid_to_render_state()
379 if (shader->CurrentProgram[MESA_SHADER_GEOMETRY]) { in _mesa_update_valid_to_render_state()
381 shader->CurrentProgram[MESA_SHADER_GEOMETRY]-> in _mesa_update_valid_to_render_state()
/third_party/mesa3d/src/amd/vulkan/
H A Dradv_pipeline.c1409 else if (radv_pipeline_has_stage(pipeline, MESA_SHADER_GEOMETRY)) in radv_compute_ia_multi_vgt_param_helpers()
1416 if (radv_pipeline_has_stage(pipeline, MESA_SHADER_GEOMETRY) && pdevice->rad_info.gfx_level <= GFX8) in radv_compute_ia_multi_vgt_param_helpers()
1423 if (radv_pipeline_has_stage(pipeline, MESA_SHADER_GEOMETRY) && pipeline->base.shaders[MESA_SHADER_GEOMETRY]->info.uses_prim_id) in radv_compute_ia_multi_vgt_param_helpers()
1438 radv_pipeline_has_stage(pipeline, MESA_SHADER_GEOMETRY)) in radv_compute_ia_multi_vgt_param_helpers()
1442 if (radv_pipeline_has_stage(pipeline, MESA_SHADER_GEOMETRY)) { in radv_compute_ia_multi_vgt_param_helpers()
1451 if (radv_pipeline_has_stage(pipeline, MESA_SHADER_GEOMETRY)) { in radv_compute_ia_multi_vgt_param_helpers()
2272 struct radv_shader_info *gs_info = &stages[MESA_SHADER_GEOMETRY].info; in gfx9_get_gs_info()
2389 stages[MESA_SHADER_GEOMETRY].info.workgroup_size = workgroup_size; in gfx9_get_gs_info()
2405 if (stages[MESA_SHADER_GEOMETRY] in radv_get_num_input_vertices()
[all...]
H A Dradv_nir_to_llvm.c136 case MESA_SHADER_GEOMETRY: in get_llvm_calling_convention()
166 stage = MESA_SHADER_GEOMETRY; in create_function()
188 (stage == MESA_SHADER_GEOMETRY && has_previous_stage)) { in create_function()
1021 if (ctx->shader_info->so.num_outputs && !ctx->args->is_gs_copy_shader && ctx->stage != MESA_SHADER_GEOMETRY) { in handle_vs_outputs_post()
1041 } else if (ctx->args->is_gs_copy_shader|| ctx->stage == MESA_SHADER_GEOMETRY) { in handle_vs_outputs_post()
1167 case MESA_SHADER_GEOMETRY: in handle_shader_outputs_post()
1216 (ctx->stage == MESA_SHADER_GEOMETRY || in ac_setup_rings()
1219 unsigned ring = ctx->stage == MESA_SHADER_GEOMETRY ? RING_ESGS_GS : RING_ESGS_VS; in ac_setup_rings()
1230 if (ctx->stage == MESA_SHADER_GEOMETRY) { in ac_setup_rings()
1414 if (ctx.stage == MESA_SHADER_GEOMETRY) { in ac_translate_nir_to_llvm()
[all...]
H A Dradv_shader_info.c74 case MESA_SHADER_GEOMETRY: in gather_intrinsic_store_output_info()
366 case MESA_SHADER_GEOMETRY: in get_vs_output_info()
389 case MESA_SHADER_GEOMETRY: in gather_info_output_decl()
504 nir->info.stage == MESA_SHADER_GEOMETRY) in radv_nir_shader_info_pass()
646 case MESA_SHADER_GEOMETRY: in radv_nir_shader_info_pass()
672 if (nir->info.stage == MESA_SHADER_GEOMETRY) { in radv_nir_shader_info_pass()
/third_party/mesa3d/src/intel/dev/
H A Dintel_device_info.c191 [MESA_SHADER_GEOMETRY] = 256,
222 [MESA_SHADER_GEOMETRY] = 256,
264 [MESA_SHADER_GEOMETRY] = 192,
293 [MESA_SHADER_GEOMETRY] = 320,
322 [MESA_SHADER_GEOMETRY] = 192,
356 [MESA_SHADER_GEOMETRY] = 256,
384 [MESA_SHADER_GEOMETRY] = 640,
412 [MESA_SHADER_GEOMETRY] = 640,
463 [MESA_SHADER_GEOMETRY] = 690,
486 [MESA_SHADER_GEOMETRY]
[all...]
/third_party/mesa3d/src/broadcom/compiler/
H A Dv3d_nir_lower_io.c126 case MESA_SHADER_GEOMETRY: in v3d_varying_slot_vpm_offset()
163 c->s->info.stage == MESA_SHADER_GEOMETRY ? in v3d_nir_lower_vpm_output()
186 assert(c->s->info.stage == MESA_SHADER_GEOMETRY); in v3d_nir_lower_vpm_output()
406 c->s->info.stage == MESA_SHADER_GEOMETRY) { in v3d_nir_lower_io_instr()
562 c->s->info.stage == MESA_SHADER_GEOMETRY ? in v3d_nir_emit_ff_vpm_outputs()
629 case MESA_SHADER_GEOMETRY: in v3d_nir_emit_ff_vpm_outputs()
706 case MESA_SHADER_GEOMETRY: in v3d_nir_lower_io()
721 if (c->s->info.stage == MESA_SHADER_GEOMETRY) in v3d_nir_lower_io()
734 } else if (s->info.stage == MESA_SHADER_GEOMETRY) { in v3d_nir_lower_io()
745 s->info.stage == MESA_SHADER_GEOMETRY) { in v3d_nir_lower_io()
[all...]
/third_party/mesa3d/src/gallium/drivers/iris/
H A Diris_pipe.h36 [PIPE_SHADER_GEOMETRY] = MESA_SHADER_GEOMETRY, in stage_from_pipe()
50 [MESA_SHADER_GEOMETRY] = PIPE_SHADER_GEOMETRY, in stage_to_pipe()
/third_party/mesa3d/src/gallium/drivers/crocus/
H A Dcrocus_pipe.h36 [PIPE_SHADER_GEOMETRY] = MESA_SHADER_GEOMETRY, in stage_from_pipe()
50 [MESA_SHADER_GEOMETRY] = PIPE_SHADER_GEOMETRY, in stage_to_pipe()
/third_party/mesa3d/src/gallium/auxiliary/tgsi/
H A Dtgsi_from_mesa.h71 case MESA_SHADER_GEOMETRY: in pipe_shader_type_from_mesa()
89 case PIPE_SHADER_GEOMETRY: return MESA_SHADER_GEOMETRY; in tgsi_processor_to_shader_stage()
/third_party/mesa3d/src/compiler/glsl/
H A Dstandalone.cpp271 ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxTextureImageUnits = 16; in initialize_context()
272 ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxUniformComponents = 1024; in initialize_context()
273 ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxCombinedUniformComponents = 1024; in initialize_context()
274 ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxInputComponents = in initialize_context()
276 ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxOutputComponents = 128; in initialize_context()
282 ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxOutputComponents; in initialize_context()
287 + ctx->Const.Program[MESA_SHADER_GEOMETRY].MaxTextureImageUnits in initialize_context()
H A Dir_set_program_inouts.cpp153 if (this->shader_stage == MESA_SHADER_GEOMETRY && in mark_whole_variable()
217 if (this->shader_stage == MESA_SHADER_GEOMETRY && in try_mark_partial_variable()
327 return stage == MESA_SHADER_GEOMETRY || in is_multiple_vertices()
/third_party/mesa3d/src/mesa/program/
H A Dprogram.h108 return MESA_SHADER_GEOMETRY; in _mesa_program_enum_to_shader_stage()
130 case MESA_SHADER_GEOMETRY: in _mesa_shader_stage_to_program()
/third_party/mesa3d/src/gallium/drivers/radeonsi/
H A Dsi_shader.c62 shader->selector->stage > MESA_SHADER_GEOMETRY) in si_is_multi_part_shader()
67 shader->selector->stage == MESA_SHADER_GEOMETRY; in si_is_multi_part_shader()
73 if (shader->selector->stage > MESA_SHADER_GEOMETRY) in si_is_merged_shader()
237 case MESA_SHADER_GEOMETRY: in si_get_max_workgroup_size()
409 if (ctx->screen->info.gfx_level >= GFX9 && stage <= MESA_SHADER_GEOMETRY) { in si_init_shader_args()
412 else if (shader->key.ge.as_es || shader->key.ge.as_ngg || stage == MESA_SHADER_GEOMETRY) in si_init_shader_args()
550 declare_per_stage_desc_pointers(ctx, ctx->stage == MESA_SHADER_GEOMETRY); in si_init_shader_args()
669 case MESA_SHADER_GEOMETRY: in si_init_shader_args()
846 (sel->stage == MESA_SHADER_GEOMETRY || in si_shader_binary_open()
847 (sel->stage <= MESA_SHADER_GEOMETRY in si_shader_binary_open()
[all...]
H A Dsi_shader_llvm.c153 if (ctx->screen->info.gfx_level >= GFX9 && ctx->stage <= MESA_SHADER_GEOMETRY) { in si_llvm_create_func()
157 real_stage = MESA_SHADER_GEOMETRY; in si_llvm_create_func()
168 case MESA_SHADER_GEOMETRY: in si_llvm_create_func()
191 if (ctx->stage <= MESA_SHADER_GEOMETRY && ctx->shader->key.ge.as_ngg && in si_llvm_create_func()
227 if (ctx->stage <= MESA_SHADER_GEOMETRY && in si_llvm_create_main_func()
395 case MESA_SHADER_GEOMETRY: in si_get_primitive_id()
824 if (ctx->stage <= MESA_SHADER_GEOMETRY && in si_llvm_translate_nir()
825 (ctx->shader->key.ge.as_es || ctx->stage == MESA_SHADER_GEOMETRY)) in si_llvm_translate_nir()
842 case MESA_SHADER_GEOMETRY: in si_llvm_translate_nir()
986 if (ctx->stage == MESA_SHADER_GEOMETRY in si_llvm_translate_nir()
[all...]
H A Dsi_state_shaders.cpp52 (stage == MESA_SHADER_GEOMETRY && !shader->key.ge.as_ngg)) in si_determine_wave_size()
120 if (stage <= MESA_SHADER_GEOMETRY && in si_determine_wave_size()
127 bool merged_shader = stage <= MESA_SHADER_GEOMETRY && shader && !shader->is_gs_copy_shader && in si_determine_wave_size()
129 stage == MESA_SHADER_TESS_CTRL || stage == MESA_SHADER_GEOMETRY); in si_determine_wave_size()
199 sel->stage == MESA_SHADER_GEOMETRY) && in si_get_ir_cache_key()
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()
1181 return sel->stage != MESA_SHADER_GEOMETRY && !shader->key.ge.opt.ngg_culling;
1301 if (gs->stage == MESA_SHADER_GEOMETRY)
[all...]
/third_party/mesa3d/src/mesa/state_tracker/
H A Dst_atom_atomicbuf.c120 st->ctx->_Shader->CurrentProgram[MESA_SHADER_GEOMETRY]; in st_bind_gs_atomics()
122 st_bind_atomics(st, prog, MESA_SHADER_GEOMETRY); in st_bind_gs_atomics()
H A Dst_program.c162 case MESA_SHADER_GEOMETRY: in st_set_prog_affected_state_flags()
286 case MESA_SHADER_GEOMETRY: in st_unbind_program()
361 nir->info.stage == MESA_SHADER_GEOMETRY) { in st_finalize_nir_before_variants()
543 case MESA_SHADER_GEOMETRY: in st_create_nir_shader()
664 } else if (nir->info.stage == MESA_SHADER_GEOMETRY) { in lower_ucp()
1231 nir->info.stage == MESA_SHADER_GEOMETRY); in st_can_add_pointsize_to_program()
1234 unsigned max_components = nir->info.stage == MESA_SHADER_GEOMETRY ? in st_can_add_pointsize_to_program()
1238 unsigned needed_components = nir->info.stage == MESA_SHADER_GEOMETRY ? nir->info.gs.vertices_out : 1; in st_can_add_pointsize_to_program()
1243 if (nir->info.stage == MESA_SHADER_GEOMETRY) { in st_can_add_pointsize_to_program()
/third_party/mesa3d/src/compiler/
H A Dshader_enums.c43 ENUM(MESA_SHADER_GEOMETRY), in gl_shader_stage_name()
70 case MESA_SHADER_GEOMETRY: return "geometry"; in _mesa_shader_stage_to_string()
98 case MESA_SHADER_GEOMETRY: return "GS"; in _mesa_shader_stage_to_abbrev()
/third_party/mesa3d/src/gallium/drivers/freedreno/ir3/
H A Dir3_cache.c107 [MESA_SHADER_GEOMETRY] = ir3_get_shader(key->gs), in ir3_cache_lookup()
159 variants[MESA_SHADER_GEOMETRY], variants[MESA_SHADER_FRAGMENT], in ir3_cache_lookup()
/third_party/mesa3d/src/intel/compiler/
H A Dbrw_vec4_gs_visitor.cpp596 const bool is_scalar = compiler->scalar_stage[MESA_SHADER_GEOMETRY]; in brw_compile_gs()
599 prog_data->base.base.stage = MESA_SHADER_GEOMETRY; in brw_compile_gs()
816 brw_print_vue_map(stderr, &c.input_vue_map, MESA_SHADER_GEOMETRY); in brw_compile_gs()
818 brw_print_vue_map(stderr, &prog_data->base.vue_map, MESA_SHADER_GEOMETRY); in brw_compile_gs()
829 &prog_data->base.base, false, MESA_SHADER_GEOMETRY); in brw_compile_gs()
H A Dbrw_compiler.c243 [MESA_SHADER_GEOMETRY] = sizeof(struct brw_gs_prog_data), in brw_prog_data_size()
267 [MESA_SHADER_GEOMETRY] = sizeof(struct brw_gs_prog_key), in brw_prog_key_size()
/third_party/mesa3d/src/gallium/frontends/lavapipe/
H A Dlvp_pipeline.c99 case MESA_SHADER_GEOMETRY: in st_shader_stage_to_ptarget()
497 nir->info.stage == MESA_SHADER_GEOMETRY) { in lvp_shader_compile_to_ir()
577 if (pipeline->pipeline_nir[MESA_SHADER_GEOMETRY]) in lvp_pipeline_xfb_init()
578 stage = MESA_SHADER_GEOMETRY; in lvp_pipeline_xfb_init()
635 case MESA_SHADER_GEOMETRY: in lvp_pipeline_compile_stage()
835 case MESA_SHADER_GEOMETRY: in lvp_graphics_pipeline_init()
836 pipeline->gs_output_lines = pipeline->pipeline_nir[MESA_SHADER_GEOMETRY] && in lvp_graphics_pipeline_init()
837 pipeline->pipeline_nir[MESA_SHADER_GEOMETRY]->info.gs.output_primitive == SHADER_PRIM_LINES; in lvp_graphics_pipeline_init()
/third_party/mesa3d/src/broadcom/common/
H A Dv3d_debug.c113 [MESA_SHADER_GEOMETRY] = V3D_DEBUG_GS, in v3d_debug_flag_for_shader_stage()

Completed in 31 milliseconds

1234567