Amy Kwan [Sun, 26 Mar 2023 04:04:53 +0000 (23:04 -0500)]
[PowerPC][GISel] Add initial GlobalISel support for vector functions.
This patch adds the initial support for vector functions and register banks
within GlobalISel. With this patch, we are able to support simple functions that
return vectors, and also functions that perform simple operations.
This patch also:
- Legalizes vector types for G_AND, G_OR, G_XOR, G_ADD, G_SUB, G_BITCAST, G_FADD, G_FSUB
- Introduce initial support for bitcasting (that will need to be extended upon)
- Add various different test cases to for test vector support within GlobalISel
Differential Revision: https://reviews.llvm.org/D137785
Amy Kwan [Sun, 26 Mar 2023 04:03:10 +0000 (23:03 -0500)]
[PowerPC] Implement 64-bit ELFv2 Calling Convention in TableGen (for integers/floats/vectors in registers)
This patch partially implements the parameter passing rules outlined in the
ELFv2 ABI within TableGen. Specifically, it implements the parameter assignment
of integers, floats, and vectors within registers - where the GPR numbering will
be "skipped" depending on the ordering of floats and vectors that appear within
a parameter list.
As we begin to adopt GlobalISel to the PowerPC backend, there is a need for a
TableGen definition that encapsulates the ELFv2 parameter passing rules. Thus,
this patch also changes the default calling convention that is returned within
the ccAssignFnForCall() function used in our GlobalISel implementation, and also
adds some additional testing of the calling convention that is implemented.
Future patches that build on top of this initial TableGen definition will aim to
add more of the ABI complexities, including support for additional types and
also in-memory arguments.
Differential Revision: https://reviews.llvm.org/D137504
Benjamin Kramer [Mon, 27 Mar 2023 12:19:18 +0000 (14:19 +0200)]
[JITLink] Drop using namespace
I don't think these are holding their weight and cause nasty to debug
compiler issues with some versions of MSVC as seen in
https://reviews.llvm.org/D144083#4220866
Just qualify the types with the full name.
Michael Maitland [Sat, 25 Mar 2023 00:16:41 +0000 (17:16 -0700)]
[RISCV] Remove UpperBound from SchedMxList and create WorstCaseBehavior records
Prior to this patch, UpperBound refered to the largest LMUL
supported. Instructions used UpperBound to assign the worst
case behaviour to records, since Instructions are not LMUL
specific. This forced the largest LMUL to have the worst case
behavior, even if that wasn't true for a subtarget.
Now that SchedWrites, SchedReads, WriteRes, and ReadAdvances
are created for (name, LMUL) pairs and (name, LMUL, SEW)
tuples, it becomes even less clear which pair should correspond
to the worst case behavior. Additionally, it no longer makes sense
for the UpperBound to belong to LMUL list and not to the SEW list.
Instead of creating a special UpperBound LMUL and an UpperBound
SEW, this patch renames UpperBound to WorstCaseBehavior, removes
it from the SchedMxList, and defines a WorstCaseBehavior SchedWrite,
SchedRead, WriteRes, and ReadAdvance for each name.
This gives subtargets the ability to describe the worst case behavior
of a record without forcing it to be the largest LMUL or the smallest
SEW.
Differential Revision: https://reviews.llvm.org/D146855
Mitch Phillips [Mon, 27 Mar 2023 11:33:53 +0000 (04:33 -0700)]
Revert "[C++20][Modules] Introduce an implementation module."
This reverts commit
c6e9823724ef6bdfee262289ee34d162db436af0.
Reason: Broke the ASan buildbots, see https://reviews.llvm.org/D126959
(the original phabricator review) for more info.
Mitch Phillips [Mon, 27 Mar 2023 11:33:09 +0000 (04:33 -0700)]
Revert "Silence unused variable warning in NDEBUG builds"
This reverts commit
8c7c1f11ffaacf762e612c65440fd2cbb58ee426.
Reason: Dependent change https://reviews.llvm.org/D126959 broke the ASan
buildbots. See that phabricator review for more comments.
Pavel Kosov [Mon, 27 Mar 2023 11:43:08 +0000 (14:43 +0300)]
[llvm-exegesis] Improve test flexibility by using available_features
Currently, all llvm-exegesis regression tests are target-specific and
they are organized so that the entire subdirectories of
llvm/test/tools/llvm-exegesis are enabled or disabled as a whole.
After the commit
e0ad2af691 ("Skip codegen" dry-run mode), at least two
kinds of tests are possible:
1) ensure that a snippet can be *generated* for the particular opcode
2) tests involving actual snippet execution inside the llvm-exegesis
process
Thus, for the particular target subdirectory, some tests should run only
on the particular host architecture and other tests only need the target
being among LLVM_TARGETS_TO_BUILD.
This commit defines a bunch of exegesis-specific features that can be
referenced in REQUIRES, UNSUPPORTED, etc. on a test-by-test basis.
~~
Huawei RRI
Reviewed By: courbet
Differential Revision: https://reviews.llvm.org/D146302
pvanhout [Mon, 27 Mar 2023 11:27:31 +0000 (13:27 +0200)]
Add Release Note for -mcode-object-v3 removal
Reviewed By: aaron.ballman
Differential Revision: https://reviews.llvm.org/D146945
Akash Banerjee [Tue, 21 Mar 2023 12:12:11 +0000 (12:12 +0000)]
[Flang][OpenMP] Added TODO checks for unsupported map types
This patch adds TODO checks for unspported types in the map clause for OpenMP Target directives.
Example of unsupported code:
implicit none
character(len=10) :: str1, str2(5,5)
type t
character(len=10) :: str1, str2(5,5)
end type t
type(t) :: v
!$omp target enter data map(to: str2(2,5))
!$omp target enter data map(to: v%str1)
!$omp target enter data map(to: v%str2)
!$omp target enter data map(to: v%str2(1,2))
end
Differential Revision: https://reviews.llvm.org/D146292
Ivan Kosarev [Mon, 27 Mar 2023 10:37:16 +0000 (11:37 +0100)]
[TableGen][GlobalISel] Support EXTRACT_SUBREGs for ComplexPattern suboperands.
This makes it possible to write GlobalISel patterns generating
EXTRACT_SUBREG instructions applied to suboperands of ComplexPattern
operands. Currently, TableGen complains that such operands are not
declared in matcher.
Reviewed By: arsenm
Differential Revision: https://reviews.llvm.org/D146800
Adrian Kuegel [Mon, 27 Mar 2023 11:03:53 +0000 (13:03 +0200)]
[mlir][ClangTidy] Remove redundant return (NFC).
Johannes de Fine Licht [Mon, 27 Mar 2023 10:38:29 +0000 (12:38 +0200)]
[MLIR][LLVM] Extend argument/result/function attribute support.
Use a disallowlist approach to deselect attributes on arguments and
return values that are not yet supported, but allow the rest to be
present when inlining.
To achieve fast lookup in `isLegalToInline`, the set of unsupported
function attributes is cached on the inliner interface object during
construction. By using a set of StringAttrs this should just amount to a
pointer lookup.
Depends on D146633
Reviewed By: gysit
Differential Revision: https://reviews.llvm.org/D146729
Nicolas Vasilache [Mon, 27 Mar 2023 10:48:21 +0000 (03:48 -0700)]
[mlir][Linalg] NFC - Move transform utilities related to subcomputation inference to Linalg/Utils
Jay Foad [Thu, 12 Jan 2023 21:02:23 +0000 (21:02 +0000)]
[MC] Store operand info immediately after the TargetInsts table. NFC.
This shrinks MCInstrDesc (and hence the whole TargetInsts table) because
we can store a 16-bit offset value to access the operands info, instead
of a pointer. This also reduces the number of relocs that need to be
applied when LLVM is compiled as position-independent code.
Differential Revision: https://reviews.llvm.org/D142219
Jay Foad [Thu, 12 Jan 2023 07:38:13 +0000 (07:38 +0000)]
[MC] Store implicit ops immediately after the TargetInsts table. NFC.
This shrinks MCInstrDesc (and hence the whole TargetInsts table) because
we can store a 16-bit offset value to access the implicit operands,
instead of a pointer. This also reduces the number of relocs that need
to be applied when LLVM is compiled as position-independent code.
Differential Revision: https://reviews.llvm.org/D142218
Tomasz Kamiński [Mon, 27 Mar 2023 08:13:20 +0000 (10:13 +0200)]
[clang] source range of variable template specialization should include initializer
This patch adjust the getSourceRange() for the
VarTemplateSpecializationDecl and VarTemplatePartialSpecializationDecl,
such that the initializer is included if present:
```
template<typename T>
T temp = 1;
template<> double temp<double> = 1;
```
This patch makes it consistent with the behavior of
non-template variables with initializers and restores
behavior that was present before https://reviews.llvm.org/D139705.
n case, when the initializer is not present we still
include the template arguments in the source range,
which was required for fixing zero-initialization fix-it.
Reviewed By: erichkeane
Differential Revision: https://reviews.llvm.org/D146733
pvanhout [Mon, 27 Mar 2023 08:15:15 +0000 (10:15 +0200)]
[AMDGPU] Remove `use-legacy-divergence-analysis`
This option has been a no-op since we switched to UA.
Reviewed By: foad
Differential Revision: https://reviews.llvm.org/D146937
Ingo Müller [Mon, 27 Mar 2023 09:23:57 +0000 (09:23 +0000)]
Revert "[mlir] Implement pass utils for 1:N type conversions."
This reverts commit
9c4611f9c7a7055b18f0a30a4c9074b9917e4ab0.
David Green [Mon, 27 Mar 2023 09:21:24 +0000 (10:21 +0100)]
[LV][ARM][AArch64] Add multi-exit Loop Vectorizer tests. NFC
These are useful to test with the various predication schemes available on
different targets.
Priyanshi Agarwal [Mon, 27 Mar 2023 08:56:35 +0000 (09:56 +0100)]
[documentation] Fix Typos
Fixes https://github.com/llvm/llvm-project/issues/56747
Patch By: ipriyanshi1708
Differential Revision: https://reviews.llvm.org/D146644
Ingo Müller [Tue, 21 Feb 2023 11:21:25 +0000 (11:21 +0000)]
[mlir] Implement pass utils for 1:N type conversions.
The current dialect conversion does not support 1:N type conversions.
This commit implements a (poor-man's) dialect conversion pass that does
just that. To keep the pass independent of the "real" dialect conversion
infrastructure, it provides a specialization of the TypeConverter class
that allows for N:1 target materializations, a specialization of the
RewritePattern and PatternRewriter classes that automatically add
appropriate unrealized casts supporting 1:N type conversions and provide
converted operands for implementing subclasses, and a conversion driver
that applies the provided patterns and replaces the unrealized casts
that haven't folded away with user-provided materializations.
The current pass is powerful enough to express many existing manual
solutions for 1:N type conversions or extend transforms that previously
didn't support them, out of which this patch implements call graph type
decomposition (which is currently implemented with a ValueDecomposer
that is only used there).
The goal of this pass is to illustrate the effect that 1:N type
conversions could have, gain experience in how patterns should be
written that achieve that effect, and get feedback on how the APIs of
the dialect conversion should be extended or changed to support such
patterns. The hope is that the "real" dialect conversion eventually
supports such patterns, at which point, this pass could be removed
again.
Reviewed By: springerm
Differential Revision: https://reviews.llvm.org/D144469
David Sherwood [Wed, 15 Mar 2023 14:25:21 +0000 (14:25 +0000)]
[LoopVectorize] Don't tail-fold for scalable VFs when there is no scalar tail
Currently in LoopVectorize we avoid tail-folding if we can
prove the trip count is always a multiple of the maximum
fixed-width VF. This works because we know the vectoriser
only ever chooses a VF that is a power of 2. However, if
we are also considering scalable VFs then we conservatively
bail out of the optimisation because we don't know the value
of vscale, which could be an odd or prime number, etc.
This patch tries to enable the same optimisation for scalable
VFs by asking if vscale is known to be a power of 2. If so,
we can then query the maximum value of vscale and use the same
logic as we do for fixed-width VFs. I've also added a new TTI
hook called isVScaleKnownToBeAPowerOfTwo that does the same
thing as the existing TargetLowering hook.
Differential Revision: https://reviews.llvm.org/D146199
Aiden Grossman [Mon, 27 Mar 2023 08:19:06 +0000 (08:19 +0000)]
[Docs][llvm-exegesis] Refactor snippet annotations in documentation
Currently, the llvm-exegesis documentation page has all
snippet annotation information under an example. This patch refactors
the annotation documentation to a separate section to make things more
clear and to make adding future annotations easier. This patch also
significantly expands the documentation on the memory scratch space to
which a pointer can be passed through a register as the documentation on
this was quite sparse previously.
Reviewed By: courbet
Differential Revision: https://reviews.llvm.org/D146890
Aiden Grossman [Mon, 27 Mar 2023 08:14:18 +0000 (08:14 +0000)]
[llvm-exegesis] Refactor InstructionBenchmark to Benchmark
When llvm-exegesis was first introduced, it only supported benchmarking
individual instructions, hence the name for the data structure storing
the data corresponding to a benchmark being called InstructionBenchmark
made sense. However, now that benchmarking arbitrary snippets is
supported, InstructionBenchmark doesn't correspond to a single
instruction. This patch refactors InstructionBenchmark to be called
Benchmark to clean up this little bit of technical debt.
Reviewed By: courbet
Differential Revision: https://reviews.llvm.org/D146884
Tomasz Kamiński [Fri, 24 Mar 2023 15:17:50 +0000 (16:17 +0100)]
[clang] Test for AST Dumping of the template variables
They illustrate unstable behavior of the https://reviews.llvm.org/D139705 after serialization.
(`#61680 <https://github.com/llvm/llvm-project/issues/61680>`).
Reviewed By: aaron.ballman
Differential Revision: https://reviews.llvm.org/D146784
Juan Manuel MARTINEZ CAAMAÑO [Fri, 24 Mar 2023 08:28:52 +0000 (09:28 +0100)]
[AMDGPU][printf] Run AMDGPUPrintfRuntimeBindingPass in -O0
AMDGPUPrintfRuntimeBindingPass is not run in the IR optimization
pipeline with -O0.
This means that with OpenCL the printf definition coming from
device_libs gets linked with the user's code, which blocks
AMDGPUPrintfRuntimeBindingPass from working after the linkage is done.
Reviewed By: arsenm
Differential Revision: https://reviews.llvm.org/D146720
pvanhout [Thu, 9 Mar 2023 09:04:50 +0000 (10:04 +0100)]
[clang] Remove legacy -m(no)-code-object-v3 options
Code object V2 and V3 have been deprecated for a long time.
They're now scheduled to be removed completely from LLVM in the coming weeks/months.
There is no reason to support those legacy options anymore as they've
also been deprecated for a long time.
Reviewed By: #amdgpu, yaxunl, artem.tamazov
Differential Revision: https://reviews.llvm.org/D145671
Sam McCall [Sat, 25 Mar 2023 03:45:35 +0000 (04:45 +0100)]
[dataflow] Delete legacy aliases
I can't find any trace of use anymore.
I'm not sure renaming the header is worth the break, but leave the FIXME.
Differential Revision: https://reviews.llvm.org/D146864
Matthias Springer [Mon, 27 Mar 2023 06:57:46 +0000 (08:57 +0200)]
[mlir][bufferize] Fix tracking of erased ops
This is a workaround until D144193 has landed.
Differential Revision: https://reviews.llvm.org/D146868
Kazu Hirata [Mon, 27 Mar 2023 06:34:13 +0000 (23:34 -0700)]
[Target] Use isNullConstant (NFC)
Yeting Kuo [Sun, 26 Mar 2023 09:01:47 +0000 (17:01 +0800)]
[RISCV] Support vector type strict_fsqrt.
Reviewed By: craig.topper
Differential Revision: https://reviews.llvm.org/D146911
Kazu Hirata [Mon, 27 Mar 2023 05:57:39 +0000 (22:57 -0700)]
[Target] Use isAllOnesConstant (NFC)
sgokhale [Mon, 27 Mar 2023 05:12:10 +0000 (10:42 +0530)]
[AArch64][CodeGen] Add few more tests for fused operations (NFC)
Add more tests to show oppurtunity for generating fused mul+add/sub ops.
Differential Revision: https://reviews.llvm.org/D146282
Lang Hames [Mon, 27 Mar 2023 04:19:25 +0000 (21:19 -0700)]
[LLJIT] Allow multiple loadPlatformDynamicLibrary calls with the same path.
Where the same dylib is loaded more than once we should just return the
JITDylib created by the first call rather than error out. This matches the
behavior of dlopen / LoadLibrary.
Brad Smith [Mon, 27 Mar 2023 03:58:16 +0000 (23:58 -0400)]
[Driver][NetBSD] Simplify NetBSD version handling
NetBSD 6.x and older is ancient. Remove now unnecessary version check.
Reviewed By: mgorny
Differential Revision: https://reviews.llvm.org/D146891
Alex Bradbury [Mon, 27 Mar 2023 03:38:16 +0000 (04:38 +0100)]
[RISCV] Allow llvm-objdump to disassemble objects with unrecognised versions of known extensions
This Moves ELFObjectFile to using
RISCVISAInfo::parseNormalizedArchString which is not an NFC, as the test
changes show. D144353 transitioned LLD to using this function, which is
specialised to parsing arch strings in the normalised format specified
in the psABI rather than user-authored strings accepted in `-march`,
which has greater flexibility.
parseNormalizedArchString does not ignore or produce an error for ISA
extensions with a version that isn't recognised/supported by LLVM. As
current GCC is marking its objects with a higher version of the A, F,
and D extensions than LLVM (see [extension versioning
discussion](https://discourse.llvm.org/t/rfc-resolving-issues-related-to-extension-versioning-in-risc-v/68472)
this massively improves the usability of llvm-objdump with such
binaries.
Differential Revision: https://reviews.llvm.org/D146114
Alex Bradbury [Mon, 27 Mar 2023 03:32:58 +0000 (04:32 +0100)]
[RISCV] Enable tools such as llvm-objdump to process objects with unrecognised base ISA versions
Tools such as llvm-objdump will currently inputs when the base ISA has
an unrecognised version. I addressed a similar issue in LLD in D144353,
introducing parseArchStringNormalized. While it would make sense to
migrate `llvm/lib/Object/ELFObjectFile.cpp` to using
`parseArchStringNormalized` as well, this patch takes a less ambitious
initial step. By tweaking the behaviour of `parseArchString` when
`IgnoreUnknown` is true (which only has one in-tree user), we use the
default supported ISA version when a base ISA with unrecognised version
is encountered.
This means that llvm-objdump and related tools will function better for
objects produced from a recent GCC. This isn't a full fix, as
IgnoreUnknown means that an imafd object with attributes specifying
newer A/F/D versions will have those extensions ignored.
Differential Revision: https://reviews.llvm.org/D146070
wangpc [Mon, 27 Mar 2023 03:24:41 +0000 (11:24 +0800)]
[TableGen] Format document
Add missing bang operators and reorder them in alphabetical order.
Reviewed By: craig.topper
Differential Revision: https://reviews.llvm.org/D146687
Younan Zhang [Sat, 25 Mar 2023 15:15:54 +0000 (23:15 +0800)]
[clangd] Fix a hover crash on unsigned 64bit value
This patch adapts to D140059, which makes an assumption that the
caller of `APSInt::getExtValue` promises no narrowing conversion
happens, i.e., from unsigned int64 to signed int64.
It also fixes clangd/clangd#1557.
Reviewed By: nridge
Differential Revision: https://reviews.llvm.org/D146874
Wang, Xin10 [Mon, 27 Mar 2023 01:29:50 +0000 (21:29 -0400)]
[X86][NFC]Remove dead code in X86ISelLowering.cpp
Look at the code in X86ISelLowering.cpp line 15579, when NumV2Elements == 0,
it has been handled in that scope, and will not move to the line 15612.
Reviewed By: RKSimon
Differential Revision: https://reviews.llvm.org/D146790
Lang Hames [Mon, 27 Mar 2023 01:13:15 +0000 (18:13 -0700)]
[LLJIT] Add convenience methods for loading dylibs and linking static libs.
LLJIT::loadPlatformDynamicLibrary loads a dynamic library at a given path
(interpreted in the executor process -- the process containing the JIT'd code),
and returns a JITDylib (whose name is the given path) that reflects the symbols
in that library. LLJIT clients wishing to make the given symbols visible to
their JIT'd code can add this JITDylib to the link order of their JITDylib(s)
using JITDylib::addToLinkOrder.
The LLJIT::linkStaticLibraryInto overloads load a static library (or universal
binary) at a given path (interpreted in the controller process -- the process
containing the LLJIT instance) and adds its symbols to the given JITDylib.
The lli tool is updated to use LLJIT::linkStaticLibraryInto to implement the
extra-archive option.
LLJIT::loadPlatformDynamicLibrary is not tested in this patch as we don't have
a good way to produce dylibs in LLVM's regression test suite.
sstwcw [Sun, 26 Mar 2023 22:42:36 +0000 (22:42 +0000)]
[clang-format] Don't squash Verilog escaped identifiers
An escaped identifier always needs a space following it so the parser
can tell it apart from the next token.
The unit tests are changed to use `FormatTestBase.h` because we need the
2-argument version of `verifyFormat`. We also added the `messUp`
virtual function because Verilog needs a different version of it.
Reviewed By: HazardyKnusperkeks
Differential Revision: https://reviews.llvm.org/D146401
Owen Pan [Tue, 21 Mar 2023 07:02:56 +0000 (00:02 -0700)]
[clang-format] Don't format already formatted integer literals
Fixes a bug in IntegerLiteralSeparatorFixer::checkSeparator() so that
only unformatted integer literals will be formatted.
Differential Revision: https://reviews.llvm.org/D146501
Lang Hames [Sun, 26 Mar 2023 18:27:54 +0000 (18:27 +0000)]
[examples] Add export_executable_symbols to HowToUseLLJIT example.
LLJIT needs access to symbols (e.g. llvm_orc_registerEHFrameSectionWrapper)
that will be defined in the executable when LLVM is linked statically.
Should fix https://github.com/llvm/llvm-project/issues/61712.
Carlos Galvez [Sun, 26 Mar 2023 13:06:37 +0000 (13:06 +0000)]
[clang-tidy] Add option to ignore user-defined literals in readability-magic-numbers
Some user-defined literals operate on implementation-defined types, like
"unsigned long long" and "long double", which are not well supported by
this check. Currently, the check gives warnings when using UDLs, without
giving possiblity to the user to whitelist common UDLs. A good compromise
until a proper fix is found (if any) is to allow the user to disable
warnings on UDLs.
Partially fixes #61656
Differential Revision: https://reviews.llvm.org/D146913
Alex Bradbury [Sun, 26 Mar 2023 15:18:47 +0000 (16:18 +0100)]
[clang][RISCV] Fix ABI lowering for _Float16 for FP ABIs
For trivial cases (`_Float16` as a standalone argument), it was
previously correctly lowered to half. But the logic for catching cases
involving structs was gated off, as at the time that logic was written
the ABI for half was unclear.
This patch fixes that and adds a release note.
Differential Revision: https://reviews.llvm.org/D145074
Alex Bradbury [Sun, 26 Mar 2023 15:11:18 +0000 (16:11 +0100)]
[clang][RISCV][test] Add test cases for empty structs and the FP calling conventions
As reported in https://github.com/llvm/llvm-project/issues/58929, Clang
currently differs from GCC in the handling of empty structs. This commit
adds some test coverage for the handling of such structs.
A follow-up patch implements a fix to match g++.
Differential Revision: https://reviews.llvm.org/D142326
Alex Bradbury [Sun, 26 Mar 2023 14:50:13 +0000 (15:50 +0100)]
[RISCV] Make RISCVISAInfo::toFeatureVector ignore unsupported extensions
parseNormalizedArchString adds a code path that creates a RISCVISAInfo
including extensions that may not be supported by LLVM (rather than
erroring or just ignoring them). Therefore, toFeatureVector needs to
check the extension is supported in order to avoid creating unrecognised
feature strings.
This change shouldn't impact any code paths used outside of test code,
but this will be relied upon by the next patch which moves llvm-objdump
and related tools over to using parseNormalizedArchString.
Differential Revision: https://reviews.llvm.org/D146113
Kadir Cetinkaya [Sun, 26 Mar 2023 14:27:52 +0000 (16:27 +0200)]
[include-cleaner] Fix crash on unresolved headers
Make sure unresolved headers are not analyzed as part of unused
includes.
Also introduces a testing fixture for analyze tests
Differential Revision: https://reviews.llvm.org/D146916
luxufan [Sun, 26 Mar 2023 14:25:21 +0000 (22:25 +0800)]
[Local] Preserve !nonnull only when K dominate J and K has a !noundef
Similar to D142687
Reviewed By: nikic
Differential Revision: https://reviews.llvm.org/D146799
LLVM GN Syncbot [Sun, 26 Mar 2023 13:35:12 +0000 (13:35 +0000)]
[gn build] Port
52296f5ed88b
Matt Arsenault [Mon, 6 Mar 2023 14:40:25 +0000 (10:40 -0400)]
AMDGPU: Add baseline test for SWDEV-380865
This demonstrates really bad rematerialization support
for 64-bit constants which need to be split into 32-bit pieces.
Matt Arsenault [Fri, 24 Mar 2023 11:21:56 +0000 (07:21 -0400)]
AMDGPU: Convert test to generated checks
Matt Arsenault [Fri, 3 Feb 2023 20:47:50 +0000 (16:47 -0400)]
InstCombine: Introduce new is.fpclass from logic of fcmp
Fixes regressions from patch to turn more classes into fcmp.
Piotr Zegar [Sun, 26 Mar 2023 13:22:43 +0000 (13:22 +0000)]
[clang-tidy] Correct union & macros handling in modernize-use-equals-default
To this moment this check were ignoring only inline
union special members, From now also out-of-line
special members going to be ignored. Also extended
support for IgnoreMacros to cover also macros used
inside a body, or used preprocesor directives.
Fixes:
- https://github.com/llvm/llvm-project/issues/28300
- https://github.com/llvm/llvm-project/issues/40554
Reviewed By: alexander-shaposhnikov
Differential Revision: https://reviews.llvm.org/D146882
Piotr Zegar [Sun, 26 Mar 2023 13:18:47 +0000 (13:18 +0000)]
[clang-tidy] Add readability-avoid-unconditional-preprocessor-if check
Check flags always enabled or disabled code blocks in preprocessor '#if'
conditions, such as '#if 0' and '#if 1' etc.
Reviewed By: carlosgalvezp
Differential Revision: https://reviews.llvm.org/D145617
Shao-Ce SUN [Thu, 23 Mar 2023 10:23:54 +0000 (18:23 +0800)]
[flang][nfc] Remove unused codes in idioms.h
Since D137859, these have not been used.
Reviewed By: Renaud-K
Differential Revision: https://reviews.llvm.org/D146709
Shoaib Meenai [Sat, 25 Mar 2023 00:34:14 +0000 (17:34 -0700)]
[ThinLTO] Only import for non-prevailing interposable global variables
This logic was added in https://reviews.llvm.org/D95943 specifically to
handle an issue for non-prevailing global variables. It turns out that
it adds a new issue for prevailing glboal variables, since those could
be replaced by an available_externally definition and hence incorrectly
omitted from the output object file. Limit the import to non-prevailing
global variables to fix this, as suggested by @tejohnson.
The bulk of the diff is mechanical changes to thread isPrevailing
through to where it's needed and ensure it's available before the
relevant calls; the actual logic change itself is straightforward.
Fixes https://github.com/llvm/llvm-project/issues/61677
Reviewed By: tejohnson
Differential Revision: https://reviews.llvm.org/D146876
Craig Topper [Sun, 26 Mar 2023 02:18:15 +0000 (19:18 -0700)]
[RISCV] Move PseudoRVVInitUndef pseudos to RISCVInstrInfoVPseudos.td. NFC
Leonard Chan [Sun, 26 Mar 2023 01:47:10 +0000 (01:47 +0000)]
Revert "[llvm] Teach GlobalDCE about dso_local_equivalent"
This reverts commit
86dbcafd0cdc88ae85896c6f12ecaa6006aeba54.
Reverting since this depends on
db288184765c0b4010060ebea1f6de3ac1f66445
which broke our lto builders reported by fxbug.dev/12380.
Leonard Chan [Sun, 26 Mar 2023 01:38:08 +0000 (01:38 +0000)]
Revert "[llvm] Teach whole program devirtualization about relative vtables"
This reverts commit
db288184765c0b4010060ebea1f6de3ac1f66445.
Reverting since it broke our lto builders reported by fxbug.dev/123807.
Emilia Dreamer [Sun, 26 Mar 2023 01:39:03 +0000 (04:39 +0300)]
[clang-format] Treat NTTP default values as expressions
clang-format already has logic to threat the right-hand side of an
equals sign. This patch applies that logic to template defaults,
which are likely to be non-template type parameters in which case the
default value should be annotated as an expression.
This should mostly only ever apply to bool and &&.
Fixes https://github.com/llvm/llvm-project/issues/61664
Reviewed By: MyDeveloperDay, owenpan
Differential Revision: https://reviews.llvm.org/D146760
Emilia Dreamer [Sun, 26 Mar 2023 01:38:42 +0000 (04:38 +0300)]
[clang-format] Don't wrap struct return types as structs
When using BraceWrapping.AfterClass or BraceWrapping.AfterStruct, the
token annotator relies on the first token of the line to determine if
we're dealing with a struct or class, however, this check is faulty if
it's actually a function with an elaborated struct/class return type, as
is common in C.
This patch skips the check if the brace is already annotated as
FunctionLBrace, in which case we already know it's a function and should
be treated as such.
Fixes https://github.com/llvm/llvm-project/issues/58527
Reviewed By: HazardyKnusperkeks, owenpan
Differential Revision: https://reviews.llvm.org/D146281
Emilia Dreamer [Sun, 26 Mar 2023 01:37:59 +0000 (04:37 +0300)]
[clang-format] Annotate lambdas with requires clauses.
The C++ grammar allows lambdas to have a *requires-clause* in two
places, either directly after the *template-parameter-list*, such as:
`[] <typename T> requires foo<T> (T t) { ... };`
Or, at the end of the *lambda-declarator* (before the lambda's body):
`[] <typename T> (T t) requires foo<T> { ... };`
Previously, these cases weren't handled at all, resulting in weird
results.
Note that this commit only handles token annotation, so the actual
formatting still ends up suboptimal. This is mostly because I do not yet
know how to approach making the requires clause formatting of lambdas
match the formatting for functions.
Fixes https://github.com/llvm/llvm-project/issues/61269
Reviewed By: HazardyKnusperkeks, owenpan
Differential Revision: https://reviews.llvm.org/D145642
lipracer [Sun, 26 Mar 2023 01:07:27 +0000 (06:37 +0530)]
[MLIR][Affine] add memory effect traits for dmaOp
DmaOp will read the source buffer and write the destination buffer so need to add some traits for it.
Reviewed By: bondhugula
Differential Revision: https://reviews.llvm.org/D144712
Craig Topper [Sun, 26 Mar 2023 00:20:08 +0000 (17:20 -0700)]
[MachineCopyPropagation] Pass DestSourcePair to isBackwardPropagatableCopy. NFC
Instead of calling isCopyInstr again, just pass the DestSourcePair
from the isCopyInstr call from the caller.
David Green [Sat, 25 Mar 2023 23:33:25 +0000 (23:33 +0000)]
[ARM] Add some tests for non-zero VCTP generation. NFC
See D146517.
Roland McGrath [Sat, 25 Mar 2023 21:30:02 +0000 (14:30 -0700)]
[libc] Add missing cast in fputil sqrt code
A cast is necessary to avoid implicit narrowing warnings
when those are enabled.
Reviewed By: abrachet
Differential Revision: https://reviews.llvm.org/D146886
Uday Bondhugula [Sat, 25 Mar 2023 22:05:03 +0000 (03:35 +0530)]
[MLIR][Affine] Fix/improve affine sibling fusion
The sibling fusion profitability checks shouldn't rely on the presence
of a store op in the sibling. The reuse is between the loads.
Fixes issues raised at https://discourse.llvm.org/t/understanding-the-affine-loop-fusion-pass/69452
Reviewed By: dcaballe
Differential Revision: https://reviews.llvm.org/D146763
Florian Hahn [Sat, 25 Mar 2023 21:30:20 +0000 (21:30 +0000)]
[Matrix] Extend test coverage for dot product lowering.
Extra tests:
* result is used by instruction
* constant vector operands
* multiply fed by other math instructions
* extra test with larger stride
Florian Hahn [Sat, 25 Mar 2023 21:23:00 +0000 (21:23 +0000)]
[Matrix] Split up dot product tests into integer and float variants.
To avoid the individual files getting too big with further additions.
sstwcw [Sat, 25 Mar 2023 21:12:49 +0000 (21:12 +0000)]
[clang-format] Handle Verilog assign statements
Reviewed By: MyDeveloperDay
Differential Revision: https://reviews.llvm.org/D146402
sstwcw [Sat, 25 Mar 2023 21:12:13 +0000 (21:12 +0000)]
[clang-format] More work on space around operators in Verilog
before:
```
(opcode *>o1) = 6.1;
a inside{b, c};
x = { >> {j}};
```
after:
```
(opcode *> o1) = 6.1;
a inside {b, c};
x = {>>{j}};
```
Reviewed By: MyDeveloperDay
Differential Revision: https://reviews.llvm.org/D146403
Anshil Gandhi [Sat, 25 Mar 2023 19:42:31 +0000 (13:42 -0600)]
[AMDGPUUnifyDivergentExitNodes] Add NewPM support
Meanwhile, use UniformityAnalysis instead of LegacyDivergenceAnalysis to collect divergence info.
Reviewed By: arsenm, sameerds
Differential Revision: https://reviews.llvm.org/D141355
Louis Dionne [Wed, 15 Mar 2023 17:46:51 +0000 (13:46 -0400)]
[clang][NFC] Fix location of 2>&1 in a few -print tests
While it's apparently valid to place Bash redirections anywhere in a
command-line, it is by far most frequently placed last. This changes
a few tests that did not conform to this convention and which I
originally thought were wrong.
Differential Revision: https://reviews.llvm.org/D146155
Louis Dionne [Sat, 25 Mar 2023 18:36:40 +0000 (14:36 -0400)]
[libc++] Add UNSUPPORTED annotations to more <format> tests on GCC 12
Those seem to have been failing for a while but we might not have noticed
because of the recent CI instability issues. I'm marking them as unsupported
to try to get the CI functional again, especially since the majority of
<format> tests are already not working on GCC 12.
Roland McGrath [Sat, 25 Mar 2023 03:29:08 +0000 (20:29 -0700)]
[libc] Define LLVM_LIBC_FUNCTION with a layer of macro expansion
Move the real LLVM_LIBC_FUNCTION macro definitions to
LLVM_LIBC_FUNCTION_IMPL and make LLVM_LIBC_FUNCTION a wrapper to
expand macros in its arguments. This makes it possible to
compile libc implementation and test files with -Dfunc=othername.
Reviewed By: sivachandra
Differential Revision: https://reviews.llvm.org/D146863
Louis Dionne [Sat, 25 Mar 2023 17:55:04 +0000 (13:55 -0400)]
[libc++][NFC] Improve documentation for running BuildKite agent locally
Aiden Grossman [Sat, 25 Mar 2023 17:15:01 +0000 (17:15 +0000)]
[Docs][llvm-mc] Add documentation on --filetype flag
Currently the filetype flag is not documented, and knowing the behavior
of this flag is fairly important for doing anything other than
disassembling to text assembly.
Reviewed By: lattner
Differential Revision: https://reviews.llvm.org/D146878
Benjamin Kramer [Sat, 25 Mar 2023 12:33:17 +0000 (13:33 +0100)]
[lldb] Move #include out of namespace lldb. NFC.
Including system headers in a namespace is not safe.
Corentin Jabot [Sat, 25 Mar 2023 12:15:08 +0000 (13:15 +0100)]
[Clang] Update DR status page to reflect Core Issues List 111.
4vtomat [Wed, 26 Oct 2022 02:09:21 +0000 (19:09 -0700)]
[RISCV] Support vector crypto extension ISA string and assembly
LLVM implements the 0.3 draft specification:
https://github.com/riscv/riscv-crypto/releases/download/v20230206/riscv-crypto-spec-vector.pdf
, and current vector crypto extension version can be found in:
https://github.com/riscv/riscv-crypto.
Differential Revision: https://reviews.llvm.org/D141672
Matthias Springer [Sat, 25 Mar 2023 11:17:45 +0000 (12:17 +0100)]
[mlir][Analysis] Fix assertion in FlatLinearConstraints
Differential Revision: https://reviews.llvm.org/D146869
Nitin John Raj [Thu, 23 Mar 2023 19:55:58 +0000 (12:55 -0700)]
[RISCV][RISCVISelLowering] Add tail agnostic policy operand to VECREDUCE instructions
Differential Revision: https://reviews.llvm.org/D146752
Nicolas Vasilache [Sat, 25 Mar 2023 07:25:28 +0000 (00:25 -0700)]
[mlir][Vector] Use a RewriterBase for IR rewrites in VectorTransferOpTransforms
Luo, Yuanke [Sat, 25 Mar 2023 01:59:31 +0000 (09:59 +0800)]
[X86] Fix the incorrect displacement for prolog/epilog
The bug is introduced in rGe4ceb5a7bb9b which set the wrong offset from
the stack base. This patch is to fix the bug.
Differential Revision: https://reviews.llvm.org/D146862
Roland McGrath [Sat, 25 Mar 2023 03:59:17 +0000 (20:59 -0700)]
[libc] Remove unused aarch64 sqrt and sqrtf implementations
These files are not used because the generic sqrt and sqrtf
functions already go through internal layers that reach the
machine-specific internal implemenations.
Reviewed By: sivachandra
Differential Revision: https://reviews.llvm.org/D146865
Craig Topper [Sat, 25 Mar 2023 02:59:12 +0000 (19:59 -0700)]
[RISCV] Make RISCVMergeBaseOffsetOpt a class instead of a struct. NFC
This lets us remove 'private:' from the top of the class.
While there collect the other private member variable at the top
of the class.
Sam McCall [Sat, 25 Mar 2023 03:32:52 +0000 (04:32 +0100)]
[Analysis] Fix use-after-scope in CFGElement dump
Sam McCall [Wed, 22 Mar 2023 12:16:17 +0000 (13:16 +0100)]
[dataflow] handle missing case in value debug strings
Differential Revision: https://reviews.llvm.org/D146625
Ye Luo [Sat, 25 Mar 2023 02:10:03 +0000 (21:10 -0500)]
Revert "[OpenMP] Ensure memory fences are created with barriers for AMDGPUs"
This reverts commit
36d6217c4eb02c15168bf74c9f7ef44ea4fb7e41.
Ye Luo [Sat, 25 Mar 2023 01:36:51 +0000 (20:36 -0500)]
[OpenMP] Ensure memory fences are created with barriers for AMDGPUs
It turns out that the `__builtin_amdgcn_s_barrier()` alone does not emit
a fence. We somehow got away with this and assumed it would work as it
(hopefully) is correct on the NVIDIA path where we just emit a
`__syncthreads`. After talking to @arsenm we now (mostly) align with the
OpenCL barrier implementation [1] and emit explicit fences for AMDGPUs.
It seems this was the underlying cause for #59759, but I am not 100%
certain. There is a chance this simply hides the problem.
Fixes: https://github.com/llvm/llvm-project/issues/59759
[1] https://github.com/RadeonOpenCompute/ROCm-Device-Libs/blob/
07b347366eb2c6ebc3414af323c623cbbbafc854/opencl/src/workgroup/wgbarrier.cl#L21
Reviewed By: ye-luo
Differential Revision: https://reviews.llvm.org/D145290
Joseph Huber [Fri, 24 Mar 2023 20:53:05 +0000 (15:53 -0500)]
[libc] Implement the RPC client / server for NVPTX
This patch adds the necessary code to impelement the existing RPC client
/ server interface when targeting NVPTX GPUs. This follows closely to
the implementation in the AMDGPU version. This does not yet enable unit
testing as the `nvlink` linker does not support static libraries. So
that will need to be worked around.
I am ignoring the RPC duplication between the AMDGPU and NVPTX loaders. This
will be changed completely later so there's no point unifying the code at this
stage. The implementation was tested manually with the following file and
compilation flags.
```
namespace __llvm_libc {
void write_to_stderr(const char *msg);
void quick_exit(int);
} // namespace __llvm_libc
using namespace __llvm_libc;
int main(int argc, char **argv, char **envp) {
for (int i = 0; i < argc; ++i) {
write_to_stderr(argv[i]);
write_to_stderr("\n");
}
quick_exit(255);
}
```
```
$ clang++ crt1.o rpc_client.o quick_exit.o io.o main.cpp --target=nvptx64-nvidia-cuda -march=sm_70 -o image
$ ./nvptx_loader image 1 2 3
image
1
2
3
$ echo $?
255
```
Depends on D146681
Reviewed By: jdoerfert
Differential Revision: https://reviews.llvm.org/D146846
Joseph Huber [Thu, 23 Mar 2023 01:00:13 +0000 (20:00 -0500)]
[libc] Add a loader utility for NVPTX architectures for testing
This patch adds a loader utility targeting the CUDA driver API to launch
NVPTX images called `nvptx_loader`. This takes a GPU image on the
command line and launches the `_start` kernel with the appropriate
arguments. The `_start` kernel is provided by the already implemented
`nvptx/start.cpp`. So, an application with a `main` function can be
compiled and run as follows.
```
clang++ --target=nvptx64-nvidia-cuda main.cpp crt1.o -march=sm_70 -o image
./nvptx_loader image args to kernel
```
This implementation is not tested and does not yet support RPC. This
requires further development to work around NVIDIA specific limitations
in atomics and linking.
Reviewed By: jdoerfert
Differential Revision: https://reviews.llvm.org/D146681
Alex Langford [Sat, 25 Mar 2023 00:53:52 +0000 (17:53 -0700)]
[lldb][NFC] Remove outdated TODO in Log.h
The code this TODO was referring to was removed in
c34698a811b137b705738b7f8d193bc896027fb8.
Alex Langford [Sat, 25 Mar 2023 00:28:13 +0000 (17:28 -0700)]
[lldb][NFC] Update and re-organize lldb-types.h
- Address the TODO by identifying and documenting all types needed by a
host system in order for lldb to work correctly
- Reformatted the comments to be easier to read
- Put everything inside of one namespace declaration instead of having
multiple of the same
- Move the macros up to be right under the accompanying definitions
Jonas Devlieghere [Sat, 25 Mar 2023 00:31:39 +0000 (17:31 -0700)]
[lldb] Remove errant call to SBReproducer.SetWorkingDirectory
The old reproducer functionality has been removed. Remove this call as
it's now just a NO-OP.
Nitin John Raj [Fri, 24 Feb 2023 21:45:31 +0000 (13:45 -0800)]
[RISCV] Made fsqrtv pseudoinstruction SEW-aware
Nitin John Raj [Fri, 24 Feb 2023 21:26:00 +0000 (13:26 -0800)]
[RISCV] Made division pseudoinstructions SEW-aware
Nitin John Raj [Fri, 24 Feb 2023 21:31:15 +0000 (13:31 -0800)]
[RISCV] Made vrgather.vv and vrgatherei16 pseudoinstructions SEW-aware