Home
last modified time | relevance | path

Searched refs:MESA_SHADER_VERTEX (Results 1 – 25 of 258) sorted by relevance

1234567891011

/third_party/mesa3d/src/compiler/glsl/
Dstandalone.cpp166 ctx->Const.Program[MESA_SHADER_VERTEX].MaxAttribs = 8; in initialize_context()
167 ctx->Const.Program[MESA_SHADER_VERTEX].MaxTextureImageUnits = 0; in initialize_context()
168 ctx->Const.Program[MESA_SHADER_VERTEX].MaxUniformComponents = 128 * 4; in initialize_context()
169 ctx->Const.Program[MESA_SHADER_VERTEX].MaxCombinedUniformComponents = 128 * 4; in initialize_context()
170 ctx->Const.Program[MESA_SHADER_VERTEX].MaxInputComponents = 0; /* not used */ in initialize_context()
171 ctx->Const.Program[MESA_SHADER_VERTEX].MaxOutputComponents = 32; in initialize_context()
178 ctx->Const.Program[MESA_SHADER_VERTEX].MaxOutputComponents; in initialize_context()
181 ctx->Const.MaxVarying = ctx->Const.Program[MESA_SHADER_VERTEX].MaxOutputComponents / 4; in initialize_context()
194 ctx->Const.Program[MESA_SHADER_VERTEX].MaxAttribs = 16; in initialize_context()
195 ctx->Const.Program[MESA_SHADER_VERTEX].MaxTextureImageUnits = 0; in initialize_context()
[all …]
Dstandalone_scaffolding.cpp111 assert(stage == MESA_SHADER_FRAGMENT || stage == MESA_SHADER_VERTEX); in _mesa_new_shader()
238 ctx->Const.Program[MESA_SHADER_VERTEX].MaxAttribs = 16; in initialize_context_to_defaults()
240 ctx->Const.Program[MESA_SHADER_VERTEX].MaxUniformComponents = 512; in initialize_context_to_defaults()
241 ctx->Const.Program[MESA_SHADER_VERTEX].MaxOutputComponents = 32; in initialize_context_to_defaults()
243 ctx->Const.Program[MESA_SHADER_VERTEX].MaxTextureImageUnits = 0; in initialize_context_to_defaults()
Dstandalone_scaffolding.h86 return MESA_SHADER_VERTEX; in _mesa_shader_enum_to_shader_stage()
99 return MESA_SHADER_VERTEX; in _mesa_shader_enum_to_shader_stage()
Dlinker.cpp2683 unsigned max_index = (target_index == MESA_SHADER_VERTEX) ? in assign_attribute_or_color_locations()
2692 assert((target_index == MESA_SHADER_VERTEX) in assign_attribute_or_color_locations()
2715 const int generic_base = (target_index == MESA_SHADER_VERTEX) in assign_attribute_or_color_locations()
2719 (target_index == MESA_SHADER_VERTEX) in assign_attribute_or_color_locations()
2767 } else if (target_index == MESA_SHADER_VERTEX) { in assign_attribute_or_color_locations()
2825 const unsigned slots = var->type->count_attribute_slots(target_index == MESA_SHADER_VERTEX); in assign_attribute_or_color_locations()
2907 const char *const string = (target_index == MESA_SHADER_VERTEX) in assign_attribute_or_color_locations()
3027 target_index == MESA_SHADER_VERTEX ? in assign_attribute_or_color_locations()
3040 if (target_index == MESA_SHADER_VERTEX) { in assign_attribute_or_color_locations()
3061 if (target_index == MESA_SHADER_VERTEX) { in assign_attribute_or_color_locations()
[all …]
/third_party/mesa3d/src/intel/common/
Dintel_urb_config.c112 for (int i = MESA_SHADER_VERTEX; i <= MESA_SHADER_GEOMETRY; i++) { in intel_get_urb_config()
123 [MESA_SHADER_VERTEX] = tess_present && devinfo->ver == 8 ? in intel_get_urb_config()
124 192 : devinfo->urb.min_entries[MESA_SHADER_VERTEX], 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()
188 for (int i = MESA_SHADER_VERTEX; 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()
[all …]
/third_party/mesa3d/src/intel/dev/
Dintel_device_info.c187 [MESA_SHADER_VERTEX] = 24,
190 [MESA_SHADER_VERTEX] = 256,
218 [MESA_SHADER_VERTEX] = 24,
221 [MESA_SHADER_VERTEX] = 256,
257 [MESA_SHADER_VERTEX] = 32,
261 [MESA_SHADER_VERTEX] = 512,
286 [MESA_SHADER_VERTEX] = 32,
290 [MESA_SHADER_VERTEX] = 704,
315 [MESA_SHADER_VERTEX] = 32,
319 [MESA_SHADER_VERTEX] = 512,
[all …]
/third_party/mesa3d/src/gallium/drivers/freedreno/ir3/
Dir3_cache.c104 [MESA_SHADER_VERTEX] = ir3_get_shader(key->vs), in ir3_cache_lookup()
114 for (gl_shader_stage stage = MESA_SHADER_VERTEX; stage < MESA_SHADER_STAGES; in ir3_cache_lookup()
126 struct ir3_compiler *compiler = shaders[MESA_SHADER_VERTEX]->compiler; in ir3_cache_lookup()
130 for (gl_shader_stage stage = MESA_SHADER_VERTEX; stage < MESA_SHADER_STAGES; in ir3_cache_lookup()
147 !!(safe_constlens & (1 << MESA_SHADER_VERTEX)); in ir3_cache_lookup()
149 ir3_shader_variant(shaders[MESA_SHADER_VERTEX], shader_key, true, debug); in ir3_cache_lookup()
153 bs = variants[MESA_SHADER_VERTEX]; in ir3_cache_lookup()
157 cache->data, bs, variants[MESA_SHADER_VERTEX], in ir3_cache_lookup()
/third_party/mesa3d/src/mesa/main/
Dshaderobj.h130 return MESA_SHADER_VERTEX; in _mesa_shader_enum_to_shader_stage()
152 case MESA_SHADER_VERTEX: in _mesa_shader_stage_to_subroutine_prefix()
174 return MESA_SHADER_VERTEX; in _mesa_shader_stage_from_subroutine_uniform()
194 return MESA_SHADER_VERTEX; in _mesa_shader_stage_from_subroutine()
214 case MESA_SHADER_VERTEX: in _mesa_shader_stage_to_subroutine()
235 case MESA_SHADER_VERTEX: in _mesa_shader_stage_to_subroutine_uniform()
Dstate.c100 ctx->_Shader->CurrentProgram[MESA_SHADER_VERTEX]; in _mesa_update_allow_draw_out_of_order()
170 ctx->_Shader->CurrentProgram[MESA_SHADER_VERTEX]; in update_program()
346 MESA_SHADER_VERTEX) | in update_program_constants()
379 !ctx->_Shader->CurrentProgram[MESA_SHADER_VERTEX] && /* GLSL */ in update_fixed_func_program_usage()
601 if (ctx->_Shader->CurrentProgram[MESA_SHADER_VERTEX]) in _mesa_update_vertex_processing_mode()
Dglspirv.c185 { MESA_SHADER_GEOMETRY, MESA_SHADER_VERTEX }, in _mesa_spirv_link_shaders()
186 { MESA_SHADER_TESS_EVAL, MESA_SHADER_VERTEX }, in _mesa_spirv_link_shaders()
187 { MESA_SHADER_TESS_CTRL, MESA_SHADER_VERTEX }, in _mesa_spirv_link_shaders()
316 if (nir->info.stage == MESA_SHADER_VERTEX) in _mesa_spirv_to_nir()
/third_party/mesa3d/src/gallium/drivers/lima/standalone/
Dlima_compiler_cmdline.c98 case MESA_SHADER_VERTEX: in load_glsl()
119 nir->info.stage == MESA_SHADER_VERTEX || in load_glsl()
142 case MESA_SHADER_VERTEX: in load_glsl()
208 stage = MESA_SHADER_VERTEX; in main()
223 case MESA_SHADER_VERTEX: in main()
/third_party/mesa3d/src/amd/vulkan/
Dradv_pipeline.c2280 : &stages[MESA_SHADER_VERTEX].info.vs.es_info; in gfx9_get_gs_info()
2384 gl_shader_stage es_stage = has_tess ? MESA_SHADER_TESS_EVAL : MESA_SHADER_VERTEX; in gfx9_get_gs_info()
2492 unsigned gs_type = stages[MESA_SHADER_GEOMETRY].nir ? MESA_SHADER_GEOMETRY : MESA_SHADER_VERTEX; in gfx10_get_ngg_info()
2561 : &stages[MESA_SHADER_VERTEX].info.so; in gfx10_get_ngg_info()
2570 …if (!stages[MESA_SHADER_TESS_CTRL].nir && stages[MESA_SHADER_VERTEX].info.vs.outinfo.export_prim_i… in gfx10_get_ngg_info()
2615 : stages[MESA_SHADER_VERTEX].info.wave_size; in gfx10_get_ngg_info()
2706 …er_stage es_stage = stages[MESA_SHADER_TESS_CTRL].nir ? MESA_SHADER_TESS_EVAL : MESA_SHADER_VERTEX; in gfx10_get_ngg_info()
2751 if (stage == MESA_SHADER_VERTEX) { in radv_get_shader()
2752 if (pipeline->shaders[MESA_SHADER_VERTEX]) in radv_get_shader()
2753 return pipeline->shaders[MESA_SHADER_VERTEX]; in radv_get_shader()
[all …]
Dradv_shader_args.c190 case MESA_SHADER_VERTEX: in allocate_user_sgprs()
196 if (previous_stage == MESA_SHADER_VERTEX) in allocate_user_sgprs()
207 if (previous_stage == MESA_SHADER_VERTEX) { in allocate_user_sgprs()
286 if (!args->is_gs_copy_shader && (stage == MESA_SHADER_VERTEX || in declare_vs_specific_input_sgprs()
287 (has_previous_stage && previous_stage == MESA_SHADER_VERTEX))) { in declare_vs_specific_input_sgprs()
361 assert(stage == MESA_SHADER_VERTEX || stage == MESA_SHADER_TESS_EVAL); in declare_streamout_sgprs()
512 if (!args->is_gs_copy_shader && (stage == MESA_SHADER_VERTEX || in set_vs_specific_input_locs()
513 (has_previous_stage && previous_stage == MESA_SHADER_VERTEX))) { in set_vs_specific_input_locs()
620 case MESA_SHADER_VERTEX: in radv_declare_shader_args()
735 if (previous_stage == MESA_SHADER_VERTEX) { in radv_declare_shader_args()
[all …]
Dradv_shader_info.c41 case MESA_SHADER_VERTEX: { in gather_intrinsic_load_input_info()
68 case MESA_SHADER_VERTEX: in gather_intrinsic_store_output_info()
332 case MESA_SHADER_VERTEX: in gather_info_input_decl()
362 case MESA_SHADER_VERTEX: in get_vs_output_info()
387 case MESA_SHADER_VERTEX: in gather_info_output_decl()
470 if (nir->info.stage == MESA_SHADER_VERTEX) { in radv_nir_shader_info_pass()
503 if (nir->info.stage == MESA_SHADER_VERTEX || nir->info.stage == MESA_SHADER_TESS_EVAL || in radv_nir_shader_info_pass()
663 case MESA_SHADER_VERTEX: in radv_nir_shader_info_pass()
680 if ((nir->info.stage == MESA_SHADER_VERTEX && info->vs.as_es) || in radv_nir_shader_info_pass()
683 nir->info.stage == MESA_SHADER_VERTEX ? &info->vs.es_info : &info->tes.es_info; in radv_nir_shader_info_pass()
[all …]
Dradv_shader.c122 for (gl_shader_stage stage = MESA_SHADER_VERTEX; stage < MESA_VULKAN_SHADER_STAGES; stage++) in radv_get_nir_options()
441 if (nir->info.stage == MESA_SHADER_VERTEX) in radv_lower_primitive_shading_rate()
444 if (nir->info.stage == MESA_SHADER_VERTEX && progress) in radv_lower_primitive_shading_rate()
506 if (nir->info.stage == MESA_SHADER_VERTEX) in radv_force_primitive_shading_rate()
510 if (nir->info.stage == MESA_SHADER_VERTEX && progress) in radv_force_primitive_shading_rate()
870 if (nir->info.stage == MESA_SHADER_VERTEX || in radv_shader_spirv_to_nir()
949 if (nir->info.stage == MESA_SHADER_VERTEX || nir->info.stage == MESA_SHADER_GEOMETRY || in radv_shader_spirv_to_nir()
1042 if ((nir->info.stage == MESA_SHADER_VERTEX || in radv_shader_spirv_to_nir()
1165 if (nir->info.stage == MESA_SHADER_VERTEX) { in radv_lower_io_to_mem()
1277 assert(nir->info.stage == MESA_SHADER_VERTEX || in radv_lower_ngg()
[all …]
/third_party/mesa3d/src/mesa/program/
Dprogram.c67 assert(ctx->Const.Program[MESA_SHADER_VERTEX].MaxUniformComponents / 4 in _mesa_init_program()
72 assert(ctx->Const.Program[MESA_SHADER_VERTEX].MaxTemps <= (1 << INST_INDEX_BITS)); in _mesa_init_program()
73 assert(ctx->Const.Program[MESA_SHADER_VERTEX].MaxLocalParams <= (1 << INST_INDEX_BITS)); in _mesa_init_program()
77 assert(ctx->Const.Program[MESA_SHADER_VERTEX].MaxUniformComponents <= 4 * MAX_UNIFORMS); in _mesa_init_program()
80 assert(ctx->Const.Program[MESA_SHADER_VERTEX].MaxAddressOffset <= (1 << INST_INDEX_BITS)); in _mesa_init_program()
228 case MESA_SHADER_VERTEX: in _mesa_new_program()
Dprogram.h102 return MESA_SHADER_VERTEX; in _mesa_program_enum_to_shader_stage()
126 case MESA_SHADER_VERTEX: in _mesa_shader_stage_to_program()
/third_party/mesa3d/src/mesa/state_tracker/
Dst_shader_cache.c83 if (prog->info.stage == MESA_SHADER_VERTEX) { in st_serialise_nir_program()
92 if (prog->info.stage == MESA_SHADER_VERTEX || in st_serialise_nir_program()
164 if (prog->info.stage == MESA_SHADER_VERTEX) { in st_deserialise_nir_program()
172 if (prog->info.stage == MESA_SHADER_VERTEX || in st_deserialise_nir_program()
Dst_program.c114 case MESA_SHADER_VERTEX: in st_set_prog_affected_state_flags()
274 case MESA_SHADER_VERTEX: in st_unbind_program()
360 nir->info.stage == MESA_SHADER_VERTEX || in st_finalize_nir_before_variants()
534 case MESA_SHADER_VERTEX: in st_create_nir_shader()
604 MESA_SHADER_VERTEX); in st_translate_vertex_program()
646 bool use_eye = st->ctx->_Shader->CurrentProgram[MESA_SHADER_VERTEX] != NULL; in lower_ucp()
660 if (nir->info.stage == MESA_SHADER_VERTEX || in lower_ucp()
809 if (prog->info.stage == MESA_SHADER_VERTEX) { in st_get_common_variant()
1229 assert(nir->info.stage == MESA_SHADER_VERTEX || in st_can_add_pointsize_to_program()
1321 if (prog->info.stage == MESA_SHADER_VERTEX) { in st_finalize_program()
/third_party/mesa3d/src/gallium/drivers/iris/
Diris_pipe.h33 [PIPE_SHADER_VERTEX] = MESA_SHADER_VERTEX, in stage_from_pipe()
47 [MESA_SHADER_VERTEX] = PIPE_SHADER_VERTEX, in stage_to_pipe()
/third_party/mesa3d/src/gallium/drivers/crocus/
Dcrocus_pipe.h33 [PIPE_SHADER_VERTEX] = MESA_SHADER_VERTEX, in stage_from_pipe()
47 [MESA_SHADER_VERTEX] = PIPE_SHADER_VERTEX, in stage_to_pipe()
/third_party/mesa3d/src/broadcom/compiler/
Dv3d_nir_lower_io.c122 case MESA_SHADER_VERTEX: in v3d_varying_slot_vpm_offset()
314 assert(c->s->info.stage == MESA_SHADER_VERTEX); in v3d_nir_lower_vertex_input()
394 if (c->s->info.stage == MESA_SHADER_VERTEX) in v3d_nir_lower_io_instr()
405 if (c->s->info.stage == MESA_SHADER_VERTEX || in v3d_nir_lower_io_instr()
626 case MESA_SHADER_VERTEX: in v3d_nir_emit_ff_vpm_outputs()
703 case MESA_SHADER_VERTEX: in v3d_nir_lower_io()
732 if (s->info.stage == MESA_SHADER_VERTEX) { in v3d_nir_lower_io()
744 if (s->info.stage == MESA_SHADER_VERTEX || in v3d_nir_lower_io()
/third_party/mesa3d/src/gallium/auxiliary/tgsi/
Dtgsi_from_mesa.h65 case MESA_SHADER_VERTEX: in pipe_shader_type_from_mesa()
88 case PIPE_SHADER_VERTEX: return MESA_SHADER_VERTEX; in tgsi_processor_to_shader_stage()
/third_party/mesa3d/src/gallium/drivers/radeonsi/
Dsi_shader.c228 case MESA_SHADER_VERTEX: in si_get_max_workgroup_size()
417 case MESA_SHADER_VERTEX: in si_init_shader_args()
494 declare_per_stage_desc_pointers(ctx, ctx->stage == MESA_SHADER_VERTEX); in si_init_shader_args()
503 if (ctx->stage == MESA_SHADER_VERTEX) in si_init_shader_args()
510 if (ctx->stage == MESA_SHADER_VERTEX) { in si_init_shader_args()
567 if (ctx->stage != MESA_SHADER_VERTEX || !shader->selector->info.base.vs.blit_sgprs_amd) { in si_init_shader_args()
569 ctx, (ctx->stage == MESA_SHADER_VERTEX || ctx->stage == MESA_SHADER_TESS_EVAL)); in si_init_shader_args()
572 if (ctx->stage == MESA_SHADER_VERTEX && shader->selector->info.base.vs.blit_sgprs_amd) { in si_init_shader_args()
577 if (ctx->stage == MESA_SHADER_VERTEX) { in si_init_shader_args()
598 if (ctx->stage == MESA_SHADER_VERTEX) in si_init_shader_args()
[all …]
/third_party/mesa3d/src/gallium/drivers/etnaviv/
Detnaviv_shader.c65 if (shader->stage == MESA_SHADER_VERTEX) in etna_dump_shader()
86 (shader->stage == MESA_SHADER_VERTEX) ? in etna_dump_shader()
94 (shader->stage == MESA_SHADER_VERTEX) ? in etna_dump_shader()
100 if (shader->stage == MESA_SHADER_VERTEX) { in etna_dump_shader()
126 assert(vs->stage == MESA_SHADER_VERTEX); in etna_link_shaders()
369 case MESA_SHADER_VERTEX: return "VERT"; in etna_shader_stage()

1234567891011