Home
last modified time | relevance | path

Searched refs:main_fn (Results 1 – 7 of 7) sorted by relevance

/third_party/mesa3d/src/gallium/drivers/radeonsi/
Dsi_shader_llvm.c183 ctx->main_fn = ac_build_main(&ctx->args, &ctx->ac, call_conv, name, ret_type, ctx->ac.module); in si_llvm_create_func()
187 ac_llvm_add_target_dep_function_attr(ctx->main_fn, "amdgpu-32bit-address-high-bits", in si_llvm_create_func()
193 ac_llvm_add_target_dep_function_attr(ctx->main_fn, "amdgpu-gds-size", 256); in si_llvm_create_func()
195 ac_llvm_set_workgroup_size(ctx->main_fn, max_workgroup_size); in si_llvm_create_func()
196 ac_llvm_set_target_features(ctx->main_fn, &ctx->ac); in si_llvm_create_func()
218 ctx->main_fn, "InitialPSInputAddr", in si_llvm_create_main_func()
320 ptr[0] = LLVMGetParam(ctx->main_fn, (merged_shader ? 8 : 0) + SI_SGPR_INTERNAL_BINDINGS); in si_prolog_get_internal_bindings()
539 LLVMValueRef param = LLVMGetParam(ctx->main_fn, i); in si_build_wrapper_function()
877 LLVMValueRef main_fn = ctx->main_fn; in si_llvm_translate_nir() local
886 values[0] = mask & 0x1 ? LLVMGetParam(main_fn, offset++) : undef; in si_llvm_translate_nir()
[all …]
Dsi_shader_llvm_ps.c209 LLVMValueRef alpha_ref = LLVMGetParam(ctx->main_fn, SI_PARAM_ALPHA_REF); in si_alpha_test()
503 builder, ret, ac_to_integer(&ctx->ac, LLVMGetParam(ctx->main_fn, SI_PARAM_ALPHA_REF)), in si_llvm_ps_build_end()
612 func = ctx->main_fn; in si_llvm_build_ps_prolog()
852 ac_llvm_add_target_dep_function_attr(ctx->main_fn, "InitialPSInputAddr", 0xffffff); in si_llvm_build_ps_epilog()
864 color[write_i][i] = LLVMGetParam(ctx->main_fn, vgpr + i / 2); in si_llvm_build_ps_epilog()
872 color[write_i][i] = LLVMGetParam(ctx->main_fn, vgpr++); in si_llvm_build_ps_epilog()
891 depth = LLVMGetParam(ctx->main_fn, vgpr_index++); in si_llvm_build_ps_epilog()
893 stencil = LLVMGetParam(ctx->main_fn, vgpr_index++); in si_llvm_build_ps_epilog()
895 samplemask = LLVMGetParam(ctx->main_fn, vgpr_index++); in si_llvm_build_ps_epilog()
937 LLVMValueRef main_fn = ctx->main_fn; in si_llvm_build_monolithic_ps() local
[all …]
Dsi_shader_llvm_vs.c59 LLVMValueRef x1y1 = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs); in load_input_vs()
60 LLVMValueRef x2y2 = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 1); in load_input_vs()
72 out[2] = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 2); in load_input_vs()
82 out[i] = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 3 + i); in load_input_vs()
86 LLVMValueRef x1 = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 3); in load_input_vs()
87 LLVMValueRef y1 = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 4); in load_input_vs()
88 LLVMValueRef x2 = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 5); in load_input_vs()
89 LLVMValueRef y2 = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 6); in load_input_vs()
93 out[2] = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 7); in load_input_vs()
94 out[3] = LLVMGetParam(ctx->main_fn, param_vs_blit_inputs + 8); in load_input_vs()
[all …]
Dsi_shader_internal.h59 LLVMValueRef main_fn; member
Dsi_shader_llvm_gs.c461 end_bb = LLVMAppendBasicBlockInContext(ctx.ac.context, ctx.main_fn, "end"); in si_generate_gs_copy_shader()
Dsi_shader_llvm_tess.c276 value[i] = LLVMGetParam(ctx->main_fn, func_param + i); in si_nir_load_tcs_varyings()
/third_party/mesa3d/src/amd/llvm/
Dac_llvm_build.c2895 LLVMValueRef main_fn = LLVMGetBasicBlockParent(LLVMGetInsertBlock(ctx->builder)); in append_basic_block() local
2896 return LLVMAppendBasicBlockInContext(ctx->context, main_fn, name); in append_basic_block()