Home
last modified time | relevance | path

Searched refs:MESA_SHADER_COMPUTE (Results 1 – 25 of 135) sorted by relevance

123456

/external/mesa3d/src/mesa/main/
Dshaderobj.h141 return MESA_SHADER_COMPUTE; in _mesa_shader_enum_to_shader_stage()
159 case MESA_SHADER_COMPUTE: in _mesa_shader_stage_to_subroutine_prefix()
181 return MESA_SHADER_COMPUTE; in _mesa_shader_stage_from_subroutine_uniform()
201 return MESA_SHADER_COMPUTE; in _mesa_shader_stage_from_subroutine()
221 case MESA_SHADER_COMPUTE: in _mesa_shader_stage_to_subroutine()
242 case MESA_SHADER_COMPUTE: in _mesa_shader_stage_to_subroutine_uniform()
Dcompute.c44 if (ctx->_Shader->CurrentProgram[MESA_SHADER_COMPUTE] == NULL) { in check_valid_to_compute()
91 struct gl_program *prog = ctx->_Shader->CurrentProgram[MESA_SHADER_COMPUTE]; in validate_DispatchCompute()
115 struct gl_program *prog = ctx->_Shader->CurrentProgram[MESA_SHADER_COMPUTE]; in validate_DispatchComputeGroupSizeARB()
271 struct gl_program *prog = ctx->_Shader->CurrentProgram[MESA_SHADER_COMPUTE]; in valid_dispatch_indirect()
/external/mesa3d/src/mesa/drivers/dri/i965/
Dbrw_cs.c137 brw_debug_recompile(brw, MESA_SHADER_COMPUTE, cp->program.Id, in brw_codegen_cs_prog()
170 (struct brw_program *) brw->programs[MESA_SHADER_COMPUTE]; in brw_cs_populate_key()
185 (struct brw_program *) brw->programs[MESA_SHADER_COMPUTE]; in brw_upload_cs_prog()
203 if (brw_disk_cache_upload_program(brw, MESA_SHADER_COMPUTE)) in brw_upload_cs_prog()
206 cp = (struct brw_program *) brw->programs[MESA_SHADER_COMPUTE]; in brw_upload_cs_prog()
Dbrw_disk_cache.c110 case MESA_SHADER_COMPUTE: in read_and_upload()
189 case MESA_SHADER_COMPUTE: in read_and_upload()
374 brw->ctx._Shader->CurrentProgram[MESA_SHADER_COMPUTE]; in brw_disk_cache_write_compute_program()
386 MESA_SHADER_COMPUTE); in brw_disk_cache_write_compute_program()
/external/mesa3d/src/gallium/drivers/iris/
Diris_pipe.h38 [PIPE_SHADER_COMPUTE] = MESA_SHADER_COMPUTE, in stage_from_pipe()
52 [MESA_SHADER_COMPUTE] = PIPE_SHADER_COMPUTE, in stage_to_pipe()
Diris_draw.c258 for (gl_shader_stage stage = 0; stage < MESA_SHADER_COMPUTE; stage++) { in iris_draw_vbo()
294 const struct iris_compiled_shader *shader = ice->shaders.prog[MESA_SHADER_COMPUTE]; in iris_update_grid_size_resource()
356 iris_predraw_resolve_inputs(ice, batch, NULL, MESA_SHADER_COMPUTE, false); in iris_launch_grid()
365 ice->state.shaders[MESA_SHADER_COMPUTE].sysvals_need_upload = true; in iris_launch_grid()
Diris_binder.c203 ice->shaders.prog[MESA_SHADER_COMPUTE]; in iris_binder_reserve_compute()
210 binder->bt_offset[MESA_SHADER_COMPUTE] = iris_binder_reserve(ice, size); in iris_binder_reserve_compute()
/external/mesa3d/src/gallium/auxiliary/tgsi/
Dtgsi_from_mesa.h75 case MESA_SHADER_COMPUTE: in pipe_shader_type_from_mesa()
92 case PIPE_SHADER_COMPUTE: return MESA_SHADER_COMPUTE; in tgsi_processor_to_shader_stage()
/external/mesa3d/src/freedreno/ir3/
Dir3_assembler.c39 shader->type = MESA_SHADER_COMPUTE; in ir3_parse_asm()
43 v->type = MESA_SHADER_COMPUTE; in ir3_parse_asm()
/external/mesa3d/src/compiler/glsl/
Dstandalone.cpp146 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxTextureImageUnits = 16; in initialize_context()
147 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxUniformComponents = 1024; in initialize_context()
148 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxCombinedUniformComponents = 1024; in initialize_context()
149 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxInputComponents = 0; /* not used */ in initialize_context()
150 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxOutputComponents = 0; /* not used */ in initialize_context()
151 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxAtomicBuffers = 8; in initialize_context()
152 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxAtomicCounters = 8; in initialize_context()
153 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxImageUniforms = 8; in initialize_context()
154 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxUniformBlocks = 12; in initialize_context()
Dstandalone_scaffolding.cpp260 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxTextureImageUnits = 16; in initialize_context_to_defaults()
261 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxUniformComponents = 1024; in initialize_context_to_defaults()
262 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxInputComponents = 0; /* not used */ in initialize_context_to_defaults()
263 ctx->Const.Program[MESA_SHADER_COMPUTE].MaxOutputComponents = 0; /* not used */ in initialize_context_to_defaults()
Dstandalone_scaffolding.h96 return MESA_SHADER_COMPUTE; in _mesa_shader_enum_to_shader_stage()
/external/mesa3d/src/mesa/program/
Dprogram.h130 return MESA_SHADER_COMPUTE; in _mesa_program_enum_to_shader_stage()
152 case MESA_SHADER_COMPUTE: in _mesa_shader_stage_to_program()
/external/mesa3d/src/intel/compiler/
Dbrw_compiler.c118 i == MESA_SHADER_FRAGMENT || i == MESA_SHADER_COMPUTE; in brw_compiler_create()
238 [MESA_SHADER_COMPUTE] = sizeof(struct brw_cs_prog_data), in brw_prog_data_size()
254 [MESA_SHADER_COMPUTE] = sizeof(struct brw_cs_prog_key), in brw_prog_key_size()
/external/mesa3d/src/mesa/state_tracker/
Dst_atom_atomicbuf.c149 st->ctx->_Shader->CurrentProgram[MESA_SHADER_COMPUTE]; in st_bind_cs_atomics()
151 st_bind_atomics(st, prog, MESA_SHADER_COMPUTE); in st_bind_cs_atomics()
/external/mesa3d/src/compiler/
Dshader_enums.c45 ENUM(MESA_SHADER_COMPUTE), in gl_shader_stage_name()
71 case MESA_SHADER_COMPUTE: return "compute"; in _mesa_shader_stage_to_string()
99 case MESA_SHADER_COMPUTE: return "CS"; in _mesa_shader_stage_to_abbrev()
Dshader_enums.h53 MESA_SHADER_COMPUTE = 5, enumerator
72 return stage == MESA_SHADER_COMPUTE || stage == MESA_SHADER_KERNEL; in gl_shader_stage_is_compute()
110 #define MESA_SHADER_STAGES (MESA_SHADER_COMPUTE + 1)
/external/mesa3d/src/gallium/frontends/lavapipe/
Dlvp_pipeline.c435 case MESA_SHADER_COMPUTE: in st_shader_stage_to_ptarget()
582 if (nir->info.stage == MESA_SHADER_COMPUTE) { in lvp_shader_compile_to_ir()
696 return MESA_SHADER_COMPUTE; in lvp_shader_stage()
709 if (stage == MESA_SHADER_COMPUTE) { in lvp_pipeline_compile()
711 shstate.prog = (void *)pipeline->pipeline_nir[MESA_SHADER_COMPUTE]; in lvp_pipeline_compile()
713 shstate.req_local_mem = pipeline->pipeline_nir[MESA_SHADER_COMPUTE]->info.cs.shared_size; in lvp_pipeline_compile()
886 MESA_SHADER_COMPUTE, in lvp_compute_pipeline_init()
888 lvp_pipeline_compile(pipeline, MESA_SHADER_COMPUTE); in lvp_compute_pipeline_init()
/external/mesa3d/src/intel/vulkan/
Danv_nir_compute_push_layout.c78 has_const_ubo && nir->info.stage != MESA_SHADER_COMPUTE; in anv_nir_compute_push_layout()
94 if (nir->info.stage == MESA_SHADER_COMPUTE) { in anv_nir_compute_push_layout()
/external/mesa3d/src/gallium/drivers/freedreno/ir3/
Dir3_cmdline.c176 case MESA_SHADER_COMPUTE: in load_glsl()
334 stage = MESA_SHADER_COMPUTE; in main()
346 stage = MESA_SHADER_COMPUTE; in main()
/external/mesa3d/src/broadcom/common/
Dv3d_debug.c73 [MESA_SHADER_COMPUTE] = V3D_DEBUG_CS, in v3d_debug_flag_for_shader_stage()
/external/mesa3d/src/gallium/drivers/freedreno/a6xx/
Dfd6_emit.h219 case MESA_SHADER_COMPUTE: in fd6_geom_stage()
247 case MESA_SHADER_COMPUTE: in fd6_stage2shadersb()
/external/mesa3d/src/compiler/nir/
Dnir_lower_point_size_mov.c72 shader->info.stage != MESA_SHADER_COMPUTE); in nir_lower_point_size_mov()
/external/mesa3d/src/compiler/spirv/tests/
Dhelpers.h62 MESA_SHADER_COMPUTE, "main", &spirv_options, &nir_options); in get_nir()
/external/mesa3d/src/amd/vulkan/
Dradv_shader.c661 if (nir->info.stage == MESA_SHADER_COMPUTE) { in radv_shader_compile_to_nir()
685 nir->info.stage != MESA_SHADER_COMPUTE) { in radv_shader_compile_to_nir()
759 if (nir->info.stage == MESA_SHADER_COMPUTE) in radv_lower_io()
1016 case MESA_SHADER_COMPUTE: in radv_postprocess_config()
1433 nir_builder_init_simple_shader(&b, NULL, MESA_SHADER_COMPUTE, NULL); in radv_create_trap_handler_shader()
1440 MESA_SHADER_COMPUTE, &info, &options, in radv_create_trap_handler_shader()
1495 case MESA_SHADER_COMPUTE: in radv_get_shader_name()
1512 case MESA_SHADER_COMPUTE: in radv_get_max_workgroup_size()
1540 } else if (stage == MESA_SHADER_COMPUTE) { in radv_get_max_waves()
1602 if (stage == MESA_SHADER_COMPUTE) { in radv_GetShaderInfoAMD()

123456