llvm-project/clang/lib/CodeGen
Weining Lu 7d88a05cc0 [Clang][LoongArch] Implement ABI lowering
Reuse most of RISCV's implementation with several exceptions:

1. Assign signext/zeroext attribute to args passed in stack.
On RISCV, integer scalars passed in registers have signext/zeroext
when promoted, but are anyext if passed on the stack. This is defined
in early RISCV ABI specification. But after this change [1], integers
should also be signext/zeroext if passed on the stack. So I think
RISCV's ABI lowering should be updated [2].

While in LoongArch ABI spec, we can see that integer scalars narrower
than GRLEN bits are zero/sign-extended no matter passed in registers
or on the stack.

2. Zero-width bit fields are ignored.
This matches GCC's behavior but it hasn't been documented in ABI sepc.
See https://gcc.gnu.org/r12-8294.

3. `char` is signed by default.
There is another difference worth mentioning is that `char` is signed
by default on LoongArch while it is unsigned on RISCV.

This patch also adds `_BitInt` type support to LoongArch and handle it
in LoongArchABIInfo::classifyArgumentType.

[1] cec39a064e
[2] https://github.com/llvm/llvm-project/issues/57261

Differential Revision: https://reviews.llvm.org/D132285
2022-09-19 12:05:00 +08:00
..
ABIInfo.h [clang][CodeGen] Factor out Swift ABI hooks (NFCI) 2022-08-08 00:23:23 +08:00
Address.h [CGOpenMPRuntime] Remove uses of deprecated Address constructor 2022-03-23 12:40:44 +01:00
BackendUtil.cpp Add -fsanitizer-coverage=control-flow 2022-09-15 15:56:04 -07:00
CGAtomic.cpp [clang-cl] Expose the /volatile:{iso,ms} choice via _ISO_VOLATILE 2022-08-23 14:29:52 +00:00
CGBlocks.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
CGBlocks.h [CodeGen] Treat ObjC `__unsafe_unretained` and class types as trivial 2022-01-11 11:18:24 -08:00
CGBuilder.h [clang] Add support for __builtin_memset_inline 2022-06-10 13:13:59 +00:00
CGBuiltin.cpp [AMDGPU] Added __builtin_amdgcn_ds_bvh_stack_rtn 2022-09-16 02:42:09 -07:00
CGCUDANV.cpp [CUDA] Allow the new driver to compile CUDA in non-RDC mode 2022-07-13 21:49:15 -04:00
CGCUDARuntime.cpp
CGCUDARuntime.h [CUDA] Create offloading entries when using the new driver 2022-05-11 07:30:21 -04:00
CGCXX.cpp [OpaquePtr] Remove uses of CGF.Builder.CreateConstInBoundsGEP1_64() without type 2021-07-17 17:07:46 +02:00
CGCXXABI.cpp [clang] CGCXXABI::EmitLoadOfMemberFunctionPointer - use castAs<> instead of getAs<> to avoid dereference of nullptr 2022-02-17 13:18:23 +00:00
CGCXXABI.h [CodeGen] Consider MangleCtx when move lazy emission States 2022-07-26 12:34:03 +08:00
CGCall.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
CGCall.h [clang][CodeGen] Only include ABIInfo.h where required (NFC) 2022-07-22 10:45:02 -07:00
CGClass.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
CGCleanup.cpp [NFC][Alignment] Use MaybeAlign in CGCleanup/CGExpr 2022-06-14 10:56:36 +00:00
CGCleanup.h [clang] Remove unused forward declarations (NFC) 2022-01-08 11:56:40 -08:00
CGCoroutine.cpp [NFC] [Frontend] Correct the use of 'auto' in SemaCoroutine and CGCoroutine 2022-09-07 10:45:01 +08:00
CGDebugInfo.cpp [clang] Fixes how we represent / emulate builtin templates 2022-09-16 17:44:12 +02:00
CGDebugInfo.h DebugInfo: Remove auto return type representation support 2022-08-17 00:35:05 +00:00
CGDecl.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
CGDeclCXX.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
CGException.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
CGExpr.cpp [clang] Use std::size instead of llvm::array_lengthof 2022-09-08 17:20:25 -06:00
CGExprAgg.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
CGExprCXX.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
CGExprComplex.cpp [clang] use getCommonSugar in an assortment of places 2022-09-16 16:36:00 +02:00
CGExprConstant.cpp [Clang] Propagate const context info when emitting compound literal 2022-08-18 11:25:20 +01:00
CGExprScalar.cpp [CodeGen] fix misnamed "not" operation; NFC 2022-08-31 15:11:48 -04:00
CGGPUBuiltin.cpp [OpenMP] Lower printf to __llvm_omp_vprintf 2021-11-10 15:30:56 +00:00
CGHLSLRuntime.cpp [HLSL]Add -O and -Od option for dxc mode. 2022-09-13 21:26:18 -07:00
CGHLSLRuntime.h [HLSL] Call global destructors from entries 2022-09-13 15:05:47 -05:00
CGLoopInfo.cpp
CGLoopInfo.h
CGNonTrivialStruct.cpp Use llvm::append_range instead of push_back loops where applicable. NFCI. 2022-03-18 01:25:34 +01:00
CGObjC.cpp [clang] Use std::size instead of llvm::array_lengthof 2022-09-08 17:20:25 -06:00
CGObjCGNU.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
CGObjCMac.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
CGObjCRuntime.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
CGObjCRuntime.h [clang][CodeGen] Only include ABIInfo.h where required (NFC) 2022-07-22 10:45:02 -07:00
CGOpenCLRuntime.cpp [CodeGen] Avoid pointer element type access for blocks 2022-03-17 16:56:31 +01:00
CGOpenCLRuntime.h [CodeGen] Avoid pointer element type access for blocks 2022-03-17 16:56:31 +01:00
CGOpenMPRuntime.cpp Revert "[OpenMP] Codegen aggregate for outlined function captures" 2022-09-15 03:08:46 +00:00
CGOpenMPRuntime.h Revert "[OpenMP] Codegen aggregate for outlined function captures" 2022-09-15 03:08:46 +00:00
CGOpenMPRuntimeGPU.cpp Revert "[OpenMP] Codegen aggregate for outlined function captures" 2022-09-15 03:08:46 +00:00
CGOpenMPRuntimeGPU.h Revert "[OpenMP] Codegen aggregate for outlined function captures" 2022-09-15 03:08:46 +00:00
CGRecordLayout.h [Clang] Add helper method to determine if a nonvirtual base has an entry in the LLVM struct 2022-03-25 16:32:12 -04:00
CGRecordLayoutBuilder.cpp [clang] Fix bugprone argument comments (NFC) 2022-01-09 00:19:49 -08:00
CGStmt.cpp [CodeGen][inlineasm] assume the flag output of inline asm is boolean value 2022-08-02 11:49:01 -07:00
CGStmtOpenMP.cpp Revert "[OpenMP] Codegen aggregate for outlined function captures" 2022-09-15 03:08:46 +00:00
CGVTT.cpp [clang codegen] Add dso_local/hidden/etc. markings to VTT declarations 2022-06-24 09:58:31 -07:00
CGVTables.cpp [clang] Do not instrument the rtti_proxies under hwasan 2022-08-26 18:22:17 +00:00
CGVTables.h [clang] Do not instrument the rtti_proxies under hwasan 2022-08-26 18:22:17 +00:00
CGValue.h [CodeGen] Store element type in RValue 2021-12-17 09:05:59 +01:00
CMakeLists.txt [HLSL][clang][Driver] Support validator version command line option. 2022-04-29 16:48:08 -07:00
CodeGenABITypes.cpp
CodeGenAction.cpp [CGDebugInfo] Access the current working directory from the `VFS` 2022-07-26 13:48:39 -07:00
CodeGenFunction.cpp Avoid __builtin_assume_aligned crash when the 1st arg is array type 2022-09-07 12:46:20 -04:00
CodeGenFunction.h Revert "[OpenMP] Codegen aggregate for outlined function captures" 2022-09-15 03:08:46 +00:00
CodeGenModule.cpp [Clang] Give error message for invalid profile path when compiling IR 2022-09-16 19:45:57 +00:00
CodeGenModule.h KCFI sanitizer 2022-08-24 22:41:38 +00:00
CodeGenPGO.cpp [InstrProf] Add the skipprofile attribute 2022-08-04 08:45:27 -07:00
CodeGenPGO.h [PGO] Don't reference functions unless value profiling is enabled 2021-05-20 11:09:24 -07:00
CodeGenTBAA.cpp [tbaa] Handle base classes in struct tbaa 2022-07-06 14:37:59 +02:00
CodeGenTBAA.h [clang] Remove unused forward declarations (NFC) 2022-01-08 11:56:40 -08:00
CodeGenTypeCache.h Fix __attribute__((annotate("")) with non-zero globals AS 2021-08-26 10:09:40 +01:00
CodeGenTypes.cpp [Clang] Allow "ext_vector_type" applied to Booleans 2022-03-16 11:10:32 +01:00
CodeGenTypes.h [clang] Properly cache member pointer LLVM types 2022-02-08 13:22:24 -08:00
ConstantEmitter.h [Clang] Propagate const context info when emitting compound literal 2022-08-18 11:25:20 +01:00
ConstantInitBuilder.cpp [clang][CodeGen] Switch a few placeholders from UndefValue to PoisonValue 2022-06-12 19:07:59 +01:00
CoverageMappingGen.cpp [Clang] Fix crash in coverage of if consteval. 2022-08-26 17:46:53 +02:00
CoverageMappingGen.h [Clang][CoverageMapping] Fix compile time explosions by adjusting only appropriated skipped ranges 2022-06-08 23:13:39 -07:00
EHScopeStack.h [Windows SEH]: HARDWARE EXCEPTION HANDLING (MSVC -EHa) - Part 1 2021-05-17 22:42:17 -07:00
ItaniumCXXABI.cpp [clang] Do not instrument relative vtables under hwasan 2022-08-26 18:21:40 +00:00
MacroPPCallbacks.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
MacroPPCallbacks.h [clang][lex] NFCI: Use FileEntryRef in PPCallbacks::InclusionDirective() 2022-04-14 10:46:12 +02:00
MicrosoftCXXABI.cpp [HLSL] Call global destructors from entries 2022-09-13 15:05:47 -05:00
ModuleBuilder.cpp [CGDebugInfo] Access the current working directory from the `VFS` 2022-07-26 13:48:39 -07:00
ObjectFilePCHContainerOperations.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
PatternInit.cpp
PatternInit.h
README.txt
SanitizerMetadata.cpp Remove 'no_sanitize_memtag'. Add 'sanitize_memtag'. 2022-07-13 08:54:41 -07:00
SanitizerMetadata.h [clang] Remove unused forward declarations (NFC) 2022-07-24 20:51:06 -07:00
SwiftCallingConv.cpp [clang] Qualify auto in range-based for loops (NFC) 2022-09-03 23:27:27 -07:00
TargetInfo.cpp [Clang][LoongArch] Implement ABI lowering 2022-09-19 12:05:00 +08:00
TargetInfo.h [clang][CodeGen] Factor out Swift ABI hooks (NFCI) 2022-08-08 00:23:23 +08:00
VarBypassDetector.cpp [clang] LLVM_FALLTHROUGH => [[fallthrough]]. NFC 2022-08-08 09:12:46 -07:00
VarBypassDetector.h Use {DenseSet,SmallPtrSet}::contains (NFC) 2021-10-29 20:26:07 -07:00

README.txt

IRgen optimization opportunities.

//===---------------------------------------------------------------------===//

The common pattern of
--
short x; // or char, etc
(x == 10)
--
generates an zext/sext of x which can easily be avoided.

//===---------------------------------------------------------------------===//

Bitfields accesses can be shifted to simplify masking and sign
extension. For example, if the bitfield width is 8 and it is
appropriately aligned then is is a lot shorter to just load the char
directly.

//===---------------------------------------------------------------------===//

It may be worth avoiding creation of alloca's for formal arguments
for the common situation where the argument is never written to or has
its address taken. The idea would be to begin generating code by using
the argument directly and if its address is taken or it is stored to
then generate the alloca and patch up the existing code.

In theory, the same optimization could be a win for block local
variables as long as the declaration dominates all statements in the
block.

NOTE: The main case we care about this for is for -O0 -g compile time
performance, and in that scenario we will need to emit the alloca
anyway currently to emit proper debug info. So this is blocked by
being able to emit debug information which refers to an LLVM
temporary, not an alloca.

//===---------------------------------------------------------------------===//

We should try and avoid generating basic blocks which only contain
jumps. At -O0, this penalizes us all the way from IRgen (malloc &
instruction overhead), all the way down through code generation and
assembly time.

On 176.gcc:expr.ll, it looks like over 12% of basic blocks are just
direct branches!

//===---------------------------------------------------------------------===//