Skip to content
Merged

v #2

Show file tree
Hide file tree
Changes from all commits
Commits
Show all changes
637 commits
Select commit Hold shift + click to select a range
e21c1b4
[gn build] Port 916e9052ba95
llvmgnsyncbot Jun 8, 2022
b3c0918
[AST] Make header self-contained
d0k Jun 8, 2022
27f970a
[Hexagon] Regenerate build-vector-v4i8-zext.ll to show full codegen
RKSimon Jun 8, 2022
a0fc94a
[MLIR][Math] Add round operation
chelini Jun 2, 2022
fd96049
[BOLT] Set valid index for functions with profiles
yota9 Jun 7, 2022
3d66330
[LV] Add test that caused revert of D123720.
fhahn Jun 8, 2022
bf21cda
Add the 2022 papers to the C status tracking page
AaronBallman Jun 8, 2022
38ad963
[sanitizer] Fix shift UB in LEB128 test
nikic Jun 8, 2022
98d4f06
Correcting some links in the C status page
AaronBallman Jun 8, 2022
cedfd7a
Recommit "[VPlan] Remove uneeded needsVectorIV check."
fhahn Jun 8, 2022
6a6f632
Revert "[RISCV] Testcase to show wrong register allocation result of …
kito-cheng Jun 8, 2022
186a0b4
M68k: Fix build
arsenm Jun 8, 2022
63aa853
[libc] Add expm1f function to bazel's build overlay.
lntue Jun 8, 2022
86a4c78
[Libomptarget] Add missing include to define `printf`
jhuber6 Jun 8, 2022
9e0dbd2
[Target] Remove `startswith` for adding `SHF_EXCLUDE` to offload section
jhuber6 Jun 8, 2022
862f30a
[RISCV] Add ISD::EH_DWARF_CFA
May 26, 2022
33ead6e
[AArch64] Add tests for bitcast high register extracts. NFC
davemgreen Jun 8, 2022
f0d2a55
Restore isa<Ty>(X) asserts inside cast<Ty>(X)
preames Jun 8, 2022
2a156f6
[Dexter] Catch value error when encountering invalid address
SLTozer Jun 6, 2022
d261d3e
[clang][NFC][SVE] Add tests for operators on VLS vectors
DavidTruby Jun 7, 2022
4f8668d
[clang] co_return cleanup
urnathan May 13, 2022
1ea9932
[RISCV] Untangle instruction properties from VSETVLIInfo [NFC]
preames Jun 8, 2022
88c1cd8
[SystemZ] Use STDY/STEY/LDY/LEY for VR32/VR64 in eliminateFrameIndex().
JonPsson Dec 8, 2021
c9677f6
[DA] Handle mismatching loop levels by considering them non-linear
bmahjour Jun 8, 2022
b84c10d
[DAG] visitVSELECT - don't wait for truncation of sub before attempti…
RKSimon Jun 8, 2022
2dfefe0
[mlir][spirv] NFC: fix typo in UnifyAliasedResourcePass pass
antiagainst Jun 8, 2022
33f4da2
[RISCV] Support LUI+ADDIW in RISCVMergeBaseOffsetOpt::matchLargeOffset.
topperc Jun 8, 2022
e4ba24c
[RISCV] Support (addi (addi globaladdr, C1), C2) in RISCVMergeBaseOff…
topperc Jun 8, 2022
9f61c8e
[SYCL] Align USM buffer location implementation for malloc_device wit…
pcolberg Jun 8, 2022
2c7caab
[SYCL] Support USM buffer location property in malloc_host (#6220)
pcolberg Jun 8, 2022
b03451b
[Dexter] Use PurePath to compare paths in Dexter commands
SLTozer Jun 6, 2022
3fcf848
[SYCL] Isolate OpenCL types and enums (#6261)
jchlanda Jun 8, 2022
51b557a
Add an error message to the default SIGPIPE handler
TNorthover May 11, 2022
9d6d069
Add a parameter to LoadFromASTFile that accepts a file system and def…
Jun 8, 2022
086a9c1
Reland [AMDGPU] gfx11 VOP1+VOP2 Instruction MC support
Sisyph May 23, 2022
e530073
[flang] Add proper todo in BoxValue
clementval Jun 8, 2022
26053cd
[WebAssembly] Regenerate simd-build-vector.ll to show full codegen
RKSimon Jun 8, 2022
d3202a5
[lldb] Parse the dotest output to determine the most appropriate resu…
JDevlieghere Jun 8, 2022
37028d3
[lldb] Update TestMultithreaded to report FAIL for a non-zero exit code
JDevlieghere Jun 8, 2022
d91735b
[flang][NFC] Move genMaxWithZero into fir:::factory
jeanPerier Jun 8, 2022
122da69
[libc] Fix build when __FE_DENORM is defined
abrachet Jun 8, 2022
a1aef4f
[AArch64] Remove ToBeRemoved from AArch64MIPeepholeOpt
davemgreen Jun 8, 2022
90668ad
[libc++] Make sure we add /llvm to the list of safe directories
ldionne Jun 8, 2022
bc99d56
[NFC][Flang][OpenMP] Refactor getting ompobject symbol
PeixinQiao Jun 8, 2022
d16a087
[LIBOMPTARGET] Adding AMD to llvm-omp-device-info
josemonsalve2 Jun 1, 2022
b6713fe
[flang] Add one semantic check for procedure bind(C) interface-name
PeixinQiao Jun 8, 2022
1f17a89
[flang] Add one missed semantic check for named constant in common block
PeixinQiao Jun 8, 2022
7611eb4
[libc++][NFC] Simplify enable_if for std::copy optimization
ldionne Jun 7, 2022
9a76337
[X86] combineMOVMSK - constant fold with getTargetConstantBitsFromNod…
RKSimon Jun 8, 2022
ea8ed5c
[mlir][sparse] Add F16 and BF16.
bixia1 Jun 7, 2022
0392d42
[libc++][NFC] Add missing 'return 0'
ldionne Jun 8, 2022
c7689fd
[Clang] Fix memory leak due to TemplateArgumentListInfo used in AST n…
browneee Jun 3, 2022
ee70039
[mlir] Fix handling of some region branch terminator successors
Mogball Jun 8, 2022
2b5e3ef
Revert "[libc++][CI] Updates Docker image."
mordante Jun 8, 2022
d6bb577
[X86] Regenerate slow-pmulld.ll with common SSE check prefixes
RKSimon Jun 8, 2022
fe9923f
[CodeView] Fix incorrect CodeView encoding of signed integer constants
stevemerr May 23, 2022
aff679a
[WebAssembly] Implement remaining relaxed SIMD instructions
tlively Jun 8, 2022
28aa7d1
[docs][clang] Minor typo fix
josemonsalve2 Jun 8, 2022
4f55ed5
Add Python bindings for the OpaqueType
dime10 Jun 8, 2022
6c6eddb
[mlir] Lower complex.power and complex.rsqrt to standard dialect.
bixia1 Jun 8, 2022
ab34ab2
[PseudoProbe] Use callee name as callsite identfier for MCDecodedPseu…
htyu May 25, 2022
288c1bf
[clang][driver] adds `-print-diagnostics`
cjdb Jun 1, 2022
40f35ce
[AMDGPU] gfx11 VOP3P instruction MC support
Sisyph May 24, 2022
7a72dca
[clang][deps] Set -disable-free for module compilations
benlangmuir Jun 7, 2022
835fcf2
[clang][deps] Make order of module dependencies deterministic
benlangmuir Jun 7, 2022
25249ab
[SYCL][Driver] Resolve conflict marker in clang/test/Driver/clang-off…
smanna12 Jun 8, 2022
7b1aa20
[MSAN] Add result printing for failed call in pthread_getaffinity_np.
kda Jun 8, 2022
49ed5bf
[clang][dataflow] Enable use of synthetic properties on all Value ins…
weiyi-t Jun 8, 2022
0371ddf
[mlir] Refactoring the tablegen Tensor types
wrengr Jun 4, 2022
fc43703
[lldb] Use objc_getRealizedClassList_trylock on macOS Ventura and later
JDevlieghere Jun 8, 2022
033af5a
[compiler-rt][hwasan] Check address tagging mode in InitializeOsSuppo…
PiJoules Jun 8, 2022
f28e48f
[cmake] Don't try creating an executable when detecting the linker
ldionne May 17, 2022
4bf9cbc
[MLIR][Presburger] subtract: improve redundant constraint detection
Superty Jun 8, 2022
4636b93
[lldb] Improve error reporting from TestAppleSimulatorOSType.py
JDevlieghere Jun 8, 2022
d897a14
[SystemZ] Fix check for zero size when lowering memcmp.
redstar Jun 2, 2022
ed6c309
[APFloat] Fix truncation of certain subnormal numbers
danilaml Jun 6, 2022
060907d
Revert "Reland "[NFC][compiler-rt][asan] Unify asan and lsan allocato…
PiJoules Jun 8, 2022
7d29374
[CSSPGO][Preinliner] Set default value of sample-profile-inline-limit…
htyu Jun 8, 2022
5d5183b
[JITLink][ELF][AArch64] Implement R_AARCH64_PREL32 and R_AARCH64_PREL64.
sunho Jun 8, 2022
56eb8dc
[compiler-rt][test] Restore original symbolize_stack test
ilovepi Jun 8, 2022
0593ce5
[MC] Add 'G' to augmentation string for MTE instrumented functions
fmayer Jun 3, 2022
4c71c33
[DWARF] Support 'G' in dwarf parser
fmayer Jun 7, 2022
b685426
Add missing entries for Annex F and Annex H to the C status page
AaronBallman Jun 8, 2022
f0a6a57
Switch links to use https consistently
AaronBallman Jun 8, 2022
14d50df
[AMDGPU] Regenerate combine-cond-add-sub.ll
RKSimon Jun 8, 2022
427ba2b
[llvm-cov] Assume repeat architectures for universal binaries
keith Mar 15, 2022
5b1c5fc
[mlir][sparse] Add complex number reading from files.
bixia1 Jun 7, 2022
40f34fe
[ELF] Support 'G' in .eh_frame
fmayer Jun 7, 2022
6fb4fe7
Revert "[ELF] Support 'G' in .eh_frame"
fmayer Jun 8, 2022
0d54a87
Revert "[DWARF] Support 'G' in dwarf parser"
fmayer Jun 8, 2022
d50dc33
[MSAN] Add comment regarding why pthread_getaffinity_np is not suppor…
kda Jun 8, 2022
dd2f290
Add llvm's Support lib to the psuedoCXX library
lanza Jun 8, 2022
d97d930
[MSAN] send output to stderr in test: pthread_getaffinity_np.
kda Jun 8, 2022
9496e39
[compiler-rt] Add the common FreeBSD AArch64 support
zxombie May 16, 2022
b3c1442
[compiler-rt] Add the FreeBSD AArch64 shadow offset
zxombie May 16, 2022
ad3fadd
[compiler-rt] Fix the longjmp sp slot on FreeBSD AArch64
zxombie May 17, 2022
ccae01c
[compiler-rt] Fix Mmap on FreeBSD AArch64
zxombie May 18, 2022
a3a7826
[mlgo] Disable accounting upon ForceStop
Northbadge Jun 8, 2022
a2695c3
[DWARF] Support 'G' in dwarf parser
fmayer Jun 8, 2022
f6b1bfb
[ELF] Support 'G' in .eh_frame
fmayer Jun 8, 2022
b8c39eb
Fix FunctionPropertiesAnalysis updating callsite in 1-BB loop
mtrofin Jun 8, 2022
93bcff8
[pseudo] Invert rows/columns of LRTable storage for speedup. NFC
sam-mccall Jun 3, 2022
bbc58c5
[pseudo] Restore accidentally removed debug print
sam-mccall Jun 8, 2022
94b2ca1
[pseudo] GC GSS nodes, reuse them with a freelist
sam-mccall May 31, 2022
4bcfc41
[SelectionDAG] Teach computeKnownBits that a nsw self multiply produc…
topperc Jun 8, 2022
ff96d43
[mlir][sparse] Fix a problem introduced by the PR for reading complex…
bixia1 Jun 8, 2022
0f02dd3
[lldb/Commands] Prevent crash due to reading memory from page zero.
chelcassanova Jun 4, 2022
c9b55eb
[lldb] Update TestModuleLoadedNotifys.py for macOS Ventura
JDevlieghere Jun 8, 2022
db313a0
[BOLT][NFC] Replace stdio with raw_ostream in CallGraph
nhuhuan Jun 8, 2022
6504b15
[libc][NFC] Mark some methods constexpr
abrachet Jun 8, 2022
0e9a01d
[libc++] Fix modules builds when features are removed
ldionne May 23, 2022
5ead1f1
[clang-format] Remove braces of else blocks that embody an if block
owenca Jun 6, 2022
ce825e4
[lldb] Add assertState function to the API test suite
JDevlieghere Jun 8, 2022
cfda534
[NFC] clang: add test for PR55886
mizvekov Jun 8, 2022
0777be6
[MSAN] print out the only possible invalid parameter (EINVAL is retur…
kda Jun 8, 2022
a1b2b7d
[clang][dataflow] Remove IndirectionValue class, moving PointeeLoc fi…
weiyi-t Jun 8, 2022
8c4d9a5
[SYCL] Query USM buffer location extension only if property is passed…
pcolberg Jun 8, 2022
d6f6cd5
[docs][clang] Fixing minor typo
josemonsalve2 Jun 8, 2022
2340b33
[SYCL][ext][CUDA] Use float as storage type for tf32 joint matrix (#5…
hdelan Jun 8, 2022
d671002
[LLDB][NativePDB] Fix several crashes when parsing debug info.
ZequanWu Jun 8, 2022
209c07d
[RISCV] Add debug message that should have been in D126843.
topperc Jun 8, 2022
3fcd366
[ORC] Add an output stream operator for SymbolStringPool.
lhames Jun 8, 2022
f4da30b
[gn build] (manually) port 0e9a01dcac99 (libcxx module.modulemap gen)
nico Jun 8, 2022
1c6dc43
[BOLT]DWARF] Eagerly write out loclists
Jun 8, 2022
aaaf8e4
Add help text for "breakpoint name", describing the feature more fully.
jimingham Jun 8, 2022
44978a2
[lld/mac] Write output sections in parallel
michaeleisel Jun 9, 2022
bf1e96d
[MicrosoftDemangle] Set error to true when returning nullptr.
ZequanWu Jun 9, 2022
a86b171
[msan][test] Use a large cpusetsize for pthread_getaffinity_np
MaskRay Jun 9, 2022
c739088
[RISCV] Fix 80 column violations in RISCVInsertVSETVLI.cpp. NFC
topperc Jun 9, 2022
2ae5232
[libc++] Towards a simpler extern template story in libc++
ldionne Jun 8, 2021
62309ed
[msan][test] Fix cpusetsize for another pthread_getaffinity_np.cpp test
MaskRay Jun 9, 2022
226c564
[InstCombine] Add vector tests for shl+lshr+and transforms; NFC
bcl5980 Jun 9, 2022
971e13d
[mlir][ods] Mark StructAttr as deprecated
Mogball Jun 9, 2022
826be33
[lld-macho] Initial support for EH Frames
int3 Jun 9, 2022
977d62c
[lld-macho] Support EH frames under arm64
int3 Jun 9, 2022
11136a6
[DeadArgElim] Remove dead code after r128810
MaskRay Jun 9, 2022
a4c97e1
[Sanitizers] prctl interception update for the PR_SET_VMA option case.
devnexen Jun 9, 2022
e6a76a4
[Clang][CoverageMapping] Fix compile time explosions by adjusting onl…
bcardosolopes Jun 8, 2022
7e17e15
clang: Introduce -fexperimental-max-bitint-width
mgehre-amd Jun 8, 2022
2a3c07f
[MLIR][Math] Re-order conversions alphabetically (NFC)
chelini Jun 9, 2022
d352017
[include-cleaner] Fix build error in unit test
ckandeler Jun 9, 2022
362a02d
[RISCV][test] Add widen STEP_VECTOR tests.
Jun 9, 2022
f971e77
ADT/ArrayRef: Add makeMutableArrayRef overloads
nhaehnle Apr 29, 2022
56c9976
[IndVarSimplify] Don't assert that terminator is not SCEVable (PR55925)
nikic Jun 8, 2022
91e31fd
[RISCV][VP] Add fp test of widen and split for vp.setcc
Jun 8, 2022
38992d2
[InstCombine] improve fold for icmp-ugt-ashr
ZCBing Jun 9, 2022
553d516
[cmake] Add missing dependencies to objlib in add_llvm_executable.
fhahn Jun 9, 2022
dc33679
[SelectionDAG] Handle bzero/memset libcalls globally instead of per t…
gchatelet Jun 8, 2022
447c411
[ARM][ParallelDSP] Fix self reference bug
sparker-arm Jun 9, 2022
fff27d1
[mlir][complex] Correctness check for complex.conj
Lewuathe Jun 9, 2022
075449d
[pseudo] Fix a sign-compare warning in debug build, NFC.
hokein Jun 9, 2022
7a05942
[pseudo] Remove the explicit Accept actions.
hokein Jun 8, 2022
40a5d79
[clang-format][NFC] Format lib/Format and unittests/Format in clang
owenca Jun 9, 2022
74e4d5f
[pseudo] Simplify the glrReduce implementation.
hokein Jun 8, 2022
ef4318e
[flang][driver] Generate run-time type info
banach-space Jun 8, 2022
5f0d4f2
[mlir] Introduce Transform ops for loops
ftynse Jun 9, 2022
8b951e6
[Flang][OpenMP] Lower schedule modifiers for worksharing loop
kiranchandramohan Jun 9, 2022
1953bcd
[flang] Add RUN lines using `fir-opt`
banach-space Jun 3, 2022
d87bfa9
[InstCombine] Combine instructions of type or/and where AND masks can…
bipmis Jun 9, 2022
4277c1b
[Attributor][FIX] Avoid metadata and duplicate replication assertion
jdoerfert Apr 13, 2022
481b8f3
[Attributor][NFC] Introduce helper struct
jdoerfert May 10, 2022
1df6e17
[Attributor] Simplify (integer range) state handling
jdoerfert May 19, 2022
7a07b88
[Attributor][FIX] Replace call site argument uses, not values
jdoerfert May 19, 2022
14899bc
[Attributor] Generalize interface from ConstantInt to Constant
jdoerfert May 19, 2022
e99e821
[FixupStatepoints] Precommit test for D127308. NFC
dantrushin Jun 9, 2022
f1ac00c
[pseudo] Add grammar annotations support.
hokein Jun 9, 2022
0840725
[Flang] Temporary fix for conversion materialization
kiranchandramohan Jun 9, 2022
afbe3ae
[clangd] Minor refactor of CanonicalIncludes::addSystemHeadersMapping.
EmployedRussian Jun 9, 2022
5160851
cmake: use llvm dir variables for clang/utils/hmaptool
mizvekov May 24, 2022
84e020a
Revert "[LIBOMPTARGET] Adding AMD to llvm-omp-device-info"
josemonsalve2 Jun 9, 2022
85983ca
[VPlan] Replace remaining use of needsScalarIV.
fhahn Jun 9, 2022
abcf149
Fix complex.conj integration test
d0k Jun 9, 2022
1a02db9
[X86] canonicalizeShuffleWithBinOps - add TODO for X86ISD::ANDNP bitw…
RKSimon Jun 9, 2022
c0e36bd
[SYCL] Fix unused value warning (#6276)
jchlanda Jun 9, 2022
264d113
AMDGPU/GISel: Introduce custom legalization of G_MUL
nhaehnle Apr 29, 2022
c8daf4a
[lldb] Add gnu-debuglink support for Windows PE/COFF
alvinhochun Jun 9, 2022
39c4ac1
[lldb] Silence a GCC warning about missing returns after a fully cove…
mstorsjo Jun 9, 2022
cb8adf7
[Attributor] Simplify loads from constant globals
jdoerfert May 19, 2022
393be12
[Attributor] Look at base values for align, nonnull, and deref
jdoerfert May 19, 2022
0ece283
[Attributor] Add checks needed as we strengthen value simplify
jdoerfert May 19, 2022
982053e
[Attributor][NFC] Improve debug code and comments
jdoerfert May 19, 2022
65b34b7
[clang][pr55896]:co_yield/co_await thread-safety
urnathan Jun 6, 2022
0abb472
AMDGPU/GISel: Remove unused variable. NFC.
d0k Jun 9, 2022
15ed5c0
[LIBOMPTARGET] Adding AMD to llvm-omp-device-info
josemonsalve2 Jun 1, 2022
9ce232f
[pseudo] Fix the missing-field-initializers warning from f1ac00c9b0d1…
hokein Jun 9, 2022
18f0b70
[pseudo] Don't clang-format test inputs. NFC
sam-mccall Jun 9, 2022
10641a4
Revert "[lld-macho] Support EH frames under arm64"
dyung Jun 9, 2022
942f4e3
Revert "[lld-macho] Initial support for EH Frames"
dyung Jun 9, 2022
b6c58ec
[mlir] add producer fusion to structured transform ops
ftynse Jun 9, 2022
bf83062
[pseudo] Fix unit test build
ckandeler Jun 9, 2022
8e1a29e
Use HTTPS links instead of HTTP ones in the C DR status page
AaronBallman Jun 9, 2022
a7bd1ab
[libc++][CI] Updates Docker image.
mordante May 30, 2022
c70aeaa
[pseudo] Move grammar-related headers to a separate dir, NFC.
hokein Jun 9, 2022
8feb92a
[clang][tests] Add missing compiler name
tbaederr Jun 9, 2022
074f12e
[OpenMP] Fix the build on Windows
JohnTitor Jun 2, 2022
cedfb54
[docs] Update supported language standards list for C++
JohnTitor Jun 5, 2022
461dafd
[mlir][bufferization] Add OneShotBufferize transform op
matthias-springer Jun 9, 2022
95141aa
Fix TableLookupTest on FreeBSD
zxombie May 18, 2022
ae10b8a
[Attributor][FIX] Give registered simplification callbacks precedence
jdoerfert Jun 9, 2022
7dbfcfa
[DAG] combineInsertEltToShuffle - if EXTRACT_VECTOR_ELT fails to matc…
RKSimon Jun 9, 2022
5ffb2ee
[Driver][SYCL] Imply -fno-discard-value-names for FPGA (#6270)
mdtoguchi Jun 9, 2022
fe2b28e
[SYCL][NFC] Refactor [[intel::reqd_sub_group_size()]] attribute tests…
smanna12 Jun 9, 2022
10c19ae
[SYCL][CUDA][HIP][libclc] Rename libclc NonUniform binops to KHR exte…
steffenlarsen Jun 9, 2022
c964961
[SYCL][CUDA][libclc] Change suld helper functions to return vectors (…
steffenlarsen Jun 9, 2022
ccaaa99
[SYCL][CUDA] Ignore and warn for mem-advise when requirement not met …
steffenlarsen Jun 9, 2022
8ae8bf2
[SYCL] Fix usage of std::conditional_variable in sycl::event (#6284)
aelovikov-intel Jun 9, 2022
f0b65a1
[Driver][SYCL] Improve deprecation messaging (#6282)
mdtoguchi Jun 9, 2022
c7e5711
[CI] Enable llvm-test-suite on CUDA Linux target (#6194)
Jun 10, 2022
0fdae34
[SYCL] Implement PI cast for vectors and fix OpenCL specializations (…
steffenlarsen Jun 10, 2022
9a31975
[SYCL][ESIMD][EMU] Replacing assert() in PI_API with return (#6275)
dongkyunahn-intel Jun 10, 2022
82b302e
Make half stream operator friend method (#6277)
AidanBeltonS Jun 10, 2022
58c9d3a
[SYCL][L0] Bump minimum shared read-only allocation slab to 2M (#6271)
smaslov-intel Jun 10, 2022
f0df89a
[SYCL][CUDA] Add experimental context and device interop (#6202)
AidanBeltonS Jun 10, 2022
567240b
Merge branch 'sycl-web' of https://github.com/otcshare/llvm into pull…
dwoodwor-intel Jun 10, 2022
69f2838
Merge commit '7dbfcfa735f28a3bd33b465c686a20c4974373ae' into pulldown…
dwoodwor-intel Jun 10, 2022
aac9f58
Change tests to use -opaque-pointers explicitly
dwoodwor-intel Jun 10, 2022
5890b66
Don't use not --crash to check for report_fatal_error messages.
jcranmer-intel May 31, 2022
df5d6d5
Disable opaque pointers when converting SPIR-V to LLVM
svenvh Jun 6, 2022
201553c
Disable opaque pointers for tests
svenvh Jun 6, 2022
49e2d09
Recover SPIR-V opaque types from demangling function names. (#1477)
jcranmer-intel Jun 7, 2022
461f493
Move pass declarations into separate header files
svenvh May 20, 2022
c4ebe56
Remove 'using namespace llvm' from some headers
svenvh Jun 8, 2022
cdf6c0a
Translate atomic_fetch_sub to OpAtomicFAddEXT with negative value ope…
haonanya1 Jun 10, 2022
1abad42
[SYCL] Separate cache dir for tests and move cache config logic (#6286)
steffenlarsen Jun 10, 2022
2c011b9
[SYCL] Add missing windows symbol for getPlugin specialization (#6291)
steffenlarsen Jun 10, 2022
7a23fb5
LLVM and SPIRV-LLVM-Translator pulldown (WW25)
bb-sycl Jun 10, 2022
3ed96a4
[SYCL][Doc] Update version of python required to build the llvm (#6293)
fineg74 Jun 10, 2022
6db064a
[SYCL][Doc] Announce ABI-breaking window (#6274)
Jun 10, 2022
9397cbc
[Driver][SYCL] Update diagnostic behavior for -fsanitize with -fsycl …
mdtoguchi Jun 11, 2022
7a2f44b
[SYCL] Fix naming and use of deprecated address spaces (#6289)
steffenlarsen Jun 11, 2022
92aadf3
[SYCL][FPGA] Add support for new attribute for loop pipelining (#6254)
smanna12 Jun 11, 2022
b59cd43
[SYCL][Doc] Initial draft of root-group proposal (#6163)
Pennycook Jun 11, 2022
8f97fe2
[SYCL] Protect access to the pi_context, pi_device and pi_platform (#…
againull Jun 13, 2022
a310952
[SYCL][libdevice] Add IMF support in devicelib (#5999)
jinge90 Jun 13, 2022
f84fc32
[SYCL] Add aspect for bfloat16 (#5720)
AidanBeltonS Jun 13, 2022
6b55f58
[SYCL][L0] Fix use of deleted scoped_lock copy constructor (#6304)
steffenlarsen Jun 14, 2022
c28f3e9
[SYCL] Adds missing get_info Windows symbol (#6305)
steffenlarsen Jun 14, 2022
4043dda
[SYCL] Bump sycl library version to 5.7.0 (#6303)
steffenlarsen Jun 14, 2022
0c7a1e1
[SYCL] Refactor SYCL kernel object handling in hierarchical paralleli…
bader Jun 15, 2022
9b4ed34
[SYCL] Keep used function declarations during llvm.used removal (#6308)
tcreech-intel Jun 15, 2022
34dcf83
[SYCL] Add support for ZEBIN format in persistent cache (#6311)
steffenlarsen Jun 15, 2022
89460e8
[SYCL][CUDA] Add experimental cuda interop with queue (#6290)
AidanBeltonS Jun 15, 2022
c4f326a
[SYCL][CUDA][PI] Improve performance of event synchronization (#6224)
t4c1 Jun 15, 2022
be1d2b2
[SYCL] Switch to using blocking free on non-GPU OpenCL devices (#6310)
sergey-semenov Jun 15, 2022
75172b1
[GHA] Uplift GPU RT version for Nightly Builds (#6299)
github-actions[bot] Jun 16, 2022
5e34cab
[ESIMD][NFC] Fix the warning "named variadic macros are a GNU extensi…
v-klochkov Jun 16, 2022
a61ac7a
[SYCL][L0][Plugin] Fix a crash in resetCommandLists (#6315)
asudarsa Jun 16, 2022
9a55da5
[ESIMD] Add set_kernel_properties API and use_double_grf property. (#…
kbobrovs Jun 17, 2022
90aaba8
[GHA] Uplift GPU RT version for Linux CI (#6300)
github-actions[bot] Jun 17, 2022
bf0fc43
[SYCL][PI] Add versioning for plugins (#6216)
hdelan Jun 17, 2022
File filter

Filter by extension

Filter by extension


Conversations
Failed to load comments.
Loading
Jump to
The table of contents is too big for display.
Diff view
Diff view
  •  
  •  
  •  
4 changes: 4 additions & 0 deletions .github/workflows/sycl_linux_build_and_test.yml
Original file line number Diff line number Diff line change
Expand Up @@ -52,6 +52,10 @@ on:
type: string
required: false
default: "ghcr.io/intel/llvm/ubuntu2004_build:latest"
cuda_image:
type: string
required: false
default: "ghcr.io/intel/llvm/ubuntu2004_build:latest"
lts_ref:
type: string
required: false
Expand Down
2 changes: 1 addition & 1 deletion .github/workflows/sycl_precommit.yml
Original file line number Diff line number Diff line change
Expand Up @@ -41,4 +41,4 @@ jobs:
build_cache_size: "8G"
build_artifact_suffix: "default"
build_cache_suffix: "default"
lts_config: "hip_amdgpu;ocl_x64;ocl_gen9;l0_gen9;esimd_emu"
lts_config: "hip_amdgpu;ocl_x64;ocl_gen9;l0_gen9;esimd_emu;cuda"
2 changes: 1 addition & 1 deletion .github/workflows/sycl_windows_build_and_test.yml
Original file line number Diff line number Diff line change
Expand Up @@ -38,7 +38,7 @@ jobs:
IF NOT EXIST D:\github\_work\cache MKDIR D:\github\_work\cache
IF NOT EXIST D:\github\_work\cache\sycl_${{inputs.build_cache_suffix}} MKDIR D:\github\_work\cache\${{inputs.build_cache_suffix}}
python.exe src/buildbot/configure.py -o build ^
--ci-default ^
--ci-defaults ^
--cmake-opt="-DCMAKE_C_COMPILER=cl" ^
--cmake-opt="-DCMAKE_CXX_COMPILER=cl" ^
--cmake-opt="-DCMAKE_INSTALL_PREFIX=%GITHUB_WORKSPACE%\install" ^
Expand Down
126 changes: 68 additions & 58 deletions bolt/include/bolt/Core/DebugData.h
Original file line number Diff line number Diff line change
Expand Up @@ -34,6 +34,30 @@ namespace llvm {

namespace bolt {

struct AttrInfo {
DWARFFormValue V;
const DWARFAbbreviationDeclaration *AbbrevDecl;
uint64_t Offset;
uint32_t Size; // Size of the attribute.
};

/// Finds attributes FormValue and Offset.
///
/// \param DIE die to look up in.
/// \param AbbrevDecl abbrev declaration for the die.
/// \param Index an index in Abbrev declaration entry.
Optional<AttrInfo>
findAttributeInfo(const DWARFDie DIE,
const DWARFAbbreviationDeclaration *AbbrevDecl,
uint32_t Index);

/// Finds attributes FormValue and Offset.
///
/// \param DIE die to look up in.
/// \param Attr the attribute to extract.
/// \return an optional AttrInfo with DWARFFormValue and Offset.
Optional<AttrInfo> findAttributeInfo(const DWARFDie DIE, dwarf::Attribute Attr);

// DWARF5 Header in order of encoding.
// Types represent encodnig sizes.
using UnitLengthType = uint32_t;
Expand Down Expand Up @@ -447,23 +471,31 @@ class DebugStrWriter {
BinaryContext &BC;
};

class DebugInfoBinaryPatcher;
class DebugAbbrevWriter;
enum class LocWriterKind { DebugLocWriter, DebugLoclistWriter };

/// Serializes part of a .debug_loc DWARF section with LocationLists.
class SimpleBinaryPatcher;
class DebugLocWriter {
protected:
DebugLocWriter(uint8_t DwarfVersion, LocWriterKind Kind)
: DwarfVersion(DwarfVersion), Kind(Kind) {
init();
}

public:
DebugLocWriter() = delete;
DebugLocWriter(BinaryContext *BC);
DebugLocWriter() { init(); };
virtual ~DebugLocWriter(){};

/// Writes out location lists and stores internal patches.
virtual void addList(uint64_t AttrOffset, uint32_t LocListIndex,
DebugLocationsVector &&LocList);
virtual void addList(AttrInfo &AttrVal, DebugLocationsVector &LocList,
DebugInfoBinaryPatcher &DebugInfoPatcher,
DebugAbbrevWriter &AbbrevWriter);

/// Writes out locations in to a local buffer, and adds Debug Info patches.
virtual void finalize(uint64_t SectionOffset,
SimpleBinaryPatcher &DebugInfoPatcher);
virtual void finalize(DebugInfoBinaryPatcher &DebugInfoPatcher,
DebugAbbrevWriter &AbbrevWriter);

/// Return internal buffer.
virtual std::unique_ptr<DebugBufferVector> getBuffer();
Expand All @@ -485,13 +517,15 @@ class DebugLocWriter {
std::unique_ptr<raw_svector_ostream> LocStream;
/// Current offset in the section (updated as new entries are written).
/// Starts with 0 here since this only writes part of a full location lists
/// section. In the final section, the first 16 bytes are reserved for an
/// empty list.
uint32_t SectionOffset{0};
/// section. In the final section, for DWARF4, the first 16 bytes are reserved
/// for an empty list.
static uint32_t LocSectionOffset;
uint8_t DwarfVersion{4};
LocWriterKind Kind{LocWriterKind::DebugLocWriter};

private:
/// Inits all the related data structures.
void init();
struct LocListDebugInfoPatchType {
uint64_t DebugInfoAttrOffset;
uint64_t LocListOffset;
Expand All @@ -501,36 +535,39 @@ class DebugLocWriter {
/// The list of debug info patches to be made once individual
/// location list writers have been filled
VectorLocListDebugInfoPatchType LocListDebugInfoPatches;

using VectorEmptyLocListAttributes = std::vector<uint64_t>;
/// Contains all the attributes pointing to empty location list.
VectorEmptyLocListAttributes EmptyAttrLists;
};

class DebugLoclistWriter : public DebugLocWriter {
public:
~DebugLoclistWriter() {}
DebugLoclistWriter() = delete;
DebugLoclistWriter(BinaryContext *BC, DWARFUnit &Unit,
uint32_t LocListsBaseAttrOffset, uint8_t DV, bool SD)
: DebugLocWriter(BC), CU(Unit),
LocListsBaseAttrOffset(LocListsBaseAttrOffset), IsSplitDwarf(SD) {
Kind = LocWriterKind::DebugLoclistWriter;
DwarfVersion = DV;
DebugLoclistWriter(DWARFUnit &Unit, uint8_t DV, bool SD)
: DebugLocWriter(DV, LocWriterKind::DebugLoclistWriter), CU(Unit),
IsSplitDwarf(SD) {
assert(DebugLoclistWriter::AddrWriter &&
"Please use SetAddressWriter to initialize "
"DebugAddrWriter before instantiation.");
if (DwarfVersion >= 5) {
LocBodyBuffer = std::make_unique<DebugBufferVector>();
LocBodyStream = std::make_unique<raw_svector_ostream>(*LocBodyBuffer);
} else {
// Writing out empty location list to which all references to empty
// location lists will point.
const char Zeroes[16] = {0};
*LocStream << StringRef(Zeroes, 16);
}
}

static void setAddressWriter(DebugAddrWriter *AddrW) { AddrWriter = AddrW; }

/// Stores location lists internally to be written out during finalize phase.
virtual void addList(uint64_t AttrOffset, uint32_t LocListIndex,
DebugLocationsVector &&LocList) override;
virtual void addList(AttrInfo &AttrVal, DebugLocationsVector &LocList,
DebugInfoBinaryPatcher &DebugInfoPatcher,
DebugAbbrevWriter &AbbrevWriter) override;

/// Writes out locations in to a local buffer and applies debug info patches.
void finalize(uint64_t SectionOffset,
SimpleBinaryPatcher &DebugInfoPatcher) override;
void finalize(DebugInfoBinaryPatcher &DebugInfoPatcher,
DebugAbbrevWriter &AbbrevWriter) override;

/// Returns CU ID.
/// For Skelton CU it is a CU Offset.
Expand All @@ -548,36 +585,21 @@ class DebugLoclistWriter : public DebugLocWriter {
bool isSplitDwarf() const { return IsSplitDwarf; }

constexpr static uint32_t InvalidIndex = UINT32_MAX;
constexpr static uint32_t InvalidLocListsBaseAttrOffset = UINT32_MAX;

private:
/// Writes out locations in to a local buffer and applies debug info patches.
void finalizeDWARFLegacy(uint64_t SectionOffset,
SimpleBinaryPatcher &DebugInfoPatcher);

/// Writes out locations in to a local buffer and applies debug info patches.
void finalizeDWARF5(uint64_t SectionOffset,
SimpleBinaryPatcher &DebugInfoPatcher);

struct LocPatch {
uint64_t AttrOffset{0};
uint32_t Index;
DebugLocationsVector LocList;
};
using LocPatchVec = SmallVector<LocPatch, 4>;
LocPatchVec Patches;
void finalizeDWARF5(DebugInfoBinaryPatcher &DebugInfoPatcher,
DebugAbbrevWriter &AbbrevWriter);

class Patch {
public:
Patch() = delete;
Patch(uint64_t O, uint64_t A) : Offset(O), Address(A) {}
uint64_t Offset{0};
uint64_t Address{0};
};
static DebugAddrWriter *AddrWriter;
DWARFUnit &CU;
uint32_t LocListsBaseAttrOffset{InvalidLocListsBaseAttrOffset};
bool IsSplitDwarf{false};
// Used for DWARF5 to store location lists before being finalized.
std::unique_ptr<DebugBufferVector> LocBodyBuffer;
std::unique_ptr<raw_svector_ostream> LocBodyStream;
std::vector<uint32_t> RelativeLocListOffsets;
uint32_t NumberOfEntries{0};
static uint32_t LoclistBaseOffset;
};

enum class PatcherKind { SimpleBinaryPatcher, DebugInfoBinaryPatcher };
Expand Down Expand Up @@ -1156,18 +1178,6 @@ class DwarfLineTable {
// Returns DWARF Version for this line table.
uint16_t getDwarfVersion() const { return DwarfVersion; }
};

struct AttrInfo {
DWARFFormValue V;
uint64_t Offset;
uint32_t Size; // Size of the attribute.
};

Optional<AttrInfo>
findAttributeInfo(const DWARFDie DIE,
const DWARFAbbreviationDeclaration *AbbrevDecl,
uint32_t Index);

} // namespace bolt
} // namespace llvm

Expand Down
2 changes: 2 additions & 0 deletions bolt/include/bolt/Passes/BinaryPasses.h
Original file line number Diff line number Diff line change
Expand Up @@ -142,6 +142,8 @@ class ReorderBasicBlocks : public BinaryFunctionPass {
/// LT_OPTIMIZE_CACHE piggybacks on the idea from Ispike paper (CGO '04)
/// that suggests putting frequently executed chains first in the layout.
LT_OPTIMIZE_CACHE,
// CACHE_PLUS and EXT_TSP are synonyms, emit warning of deprecation.
LT_OPTIMIZE_CACHE_PLUS,
/// Block reordering guided by the extended TSP metric.
LT_OPTIMIZE_EXT_TSP,
/// Create clusters and use random order for them.
Expand Down
27 changes: 14 additions & 13 deletions bolt/include/bolt/Passes/CallGraph.h
Original file line number Diff line number Diff line change
Expand Up @@ -9,9 +9,10 @@
#ifndef BOLT_PASSES_CALLGRAPH_H
#define BOLT_PASSES_CALLGRAPH_H

#include "llvm/Support/FileSystem.h"
#include "llvm/Support/raw_ostream.h"
#include <cassert>
#include <cstdint>
#include <cstdio>
#include <unordered_set>
#include <vector>

Expand Down Expand Up @@ -160,31 +161,31 @@ class CallGraph {
};

template <class L> void CallGraph::printDot(char *FileName, L GetLabel) const {
FILE *File = fopen(FileName, "wt");
if (!File)
std::error_code EC;
raw_fd_ostream OS(std::string(FileName), EC, sys::fs::OF_None);
if (EC)
return;

fprintf(File, "digraph g {\n");
OS << "digraph g {\n";
for (NodeId F = 0; F < Nodes.size(); F++) {
if (Nodes[F].samples() == 0)
continue;
fprintf(File, "f%lu [label=\"%s\\nsamples=%u\\nsize=%u\"];\n", F,
GetLabel(F), Nodes[F].samples(), Nodes[F].size());
OS << "f" << F << " [label=\"" << GetLabel(F)
<< "\\nsamples=" << Nodes[F].samples() << "\\nsize=" << Nodes[F].size()
<< "\"];\n";
}
for (NodeId F = 0; F < Nodes.size(); F++) {
if (Nodes[F].samples() == 0)
continue;
for (NodeId Dst : Nodes[F].successors()) {
ArcConstIterator Arc = findArc(F, Dst);
fprintf(
File,
"f%lu -> f%u [label=\"normWgt=%.3lf,weight=%.0lf,callOffset=%.1lf\"];"
"\n",
F, Dst, Arc->normalizedWeight(), Arc->weight(), Arc->avgCallOffset());
OS << "f" << F << " -> f" << Dst
<< " [label=\"normWgt=" << format("%.3lf", Arc->normalizedWeight())
<< ",weight=" << format("%.0lf", Arc->weight())
<< ",callOffset=" << format("%.1lf", Arc->avgCallOffset()) << "\"];\n";
}
}
fprintf(File, "}\n");
fclose(File);
OS << "}\n";
}

} // namespace bolt
Expand Down
2 changes: 1 addition & 1 deletion bolt/include/bolt/Rewrite/DWARFRewriter.h
Original file line number Diff line number Diff line change
Expand Up @@ -112,7 +112,7 @@ class DWARFRewriter {
Optional<uint64_t> RangesBase = None);

std::unique_ptr<DebugBufferVector>
makeFinalLocListsSection(SimpleBinaryPatcher &DebugInfoPatcher,
makeFinalLocListsSection(DebugInfoBinaryPatcher &DebugInfoPatcher,
DWARFVersion Version);

/// Finalize debug sections in the main binary.
Expand Down
19 changes: 7 additions & 12 deletions bolt/lib/Core/BinaryContext.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -47,12 +47,9 @@ using namespace llvm;

namespace opts {

cl::opt<bool>
NoHugePages("no-huge-pages",
cl::desc("use regular size pages for code alignment"),
cl::ZeroOrMore,
cl::Hidden,
cl::cat(BoltCategory));
cl::opt<bool> NoHugePages("no-huge-pages",
cl::desc("use regular size pages for code alignment"),
cl::Hidden, cl::cat(BoltCategory));

static cl::opt<bool>
PrintDebugInfo("print-debug-info",
Expand All @@ -61,12 +58,10 @@ PrintDebugInfo("print-debug-info",
cl::ZeroOrMore,
cl::cat(BoltCategory));

cl::opt<bool>
PrintRelocations("print-relocations",
cl::desc("print relocations when printing functions/objects"),
cl::Hidden,
cl::ZeroOrMore,
cl::cat(BoltCategory));
cl::opt<bool> PrintRelocations(
"print-relocations",
cl::desc("print relocations when printing functions/objects"), cl::Hidden,
cl::cat(BoltCategory));

static cl::opt<bool>
PrintMemData("print-mem-data",
Expand Down
8 changes: 3 additions & 5 deletions bolt/lib/Core/BinaryData.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -25,11 +25,9 @@ extern cl::OptionCategory BoltCategory;
extern cl::opt<unsigned> Verbosity;

cl::opt<bool>
PrintSymbolAliases("print-aliases",
cl::desc("print aliases when printing objects"),
cl::Hidden,
cl::ZeroOrMore,
cl::cat(BoltCategory));
PrintSymbolAliases("print-aliases",
cl::desc("print aliases when printing objects"),
cl::Hidden, cl::cat(BoltCategory));
}

bool BinaryData::isAbsolute() const { return Flags & SymbolRef::SF_Absolute; }
Expand Down
29 changes: 10 additions & 19 deletions bolt/lib/Core/BinaryEmitter.cpp
Original file line number Diff line number Diff line change
Expand Up @@ -34,12 +34,8 @@ namespace opts {
extern cl::opt<JumpTableSupportLevel> JumpTables;
extern cl::opt<bool> PreserveBlocksAlignment;

cl::opt<bool>
AlignBlocks("align-blocks",
cl::desc("align basic blocks"),
cl::init(false),
cl::ZeroOrMore,
cl::cat(BoltOptCategory));
cl::opt<bool> AlignBlocks("align-blocks", cl::desc("align basic blocks"),
cl::cat(BoltOptCategory));

cl::opt<MacroFusionType>
AlignMacroOpFusion("align-macro-fusion",
Expand Down Expand Up @@ -70,20 +66,15 @@ FunctionPadSpec("pad-funcs",
cl::Hidden,
cl::cat(BoltCategory));

static cl::opt<bool>
MarkFuncs("mark-funcs",
cl::desc("mark function boundaries with break instruction to make "
"sure we accidentally don't cross them"),
cl::ReallyHidden,
cl::ZeroOrMore,
cl::cat(BoltCategory));
static cl::opt<bool> MarkFuncs(
"mark-funcs",
cl::desc("mark function boundaries with break instruction to make "
"sure we accidentally don't cross them"),
cl::ReallyHidden, cl::cat(BoltCategory));

static cl::opt<bool>
PrintJumpTables("print-jump-tables",
cl::desc("print jump tables"),
cl::ZeroOrMore,
cl::Hidden,
cl::cat(BoltCategory));
static cl::opt<bool> PrintJumpTables("print-jump-tables",
cl::desc("print jump tables"), cl::Hidden,
cl::cat(BoltCategory));

static cl::opt<bool>
X86AlignBranchBoundaryHotOnly("x86-align-branch-boundary-hot-only",
Expand Down
Loading