summaryrefslogtreecommitdiffstats
Commit message (Collapse)AuthorAgeFilesLines
* Disable the vzeroupper insertion pass on PS4.Yunzhong Gao2016-02-022-0/+12
| | | | | | | | See comments in test/CodeGen/X86/avx-vzeroupper.ll for more explanation. Original patch by: Sean Silva llvm-svn: 259576
* [Orc] Stub addresses should be based on stub size, not pointer size.Lang Hames2016-02-021-1/+1
| | | | | | | | This didn't affect X86_64, which is the only client of this code at the moment, as stubs and pointers are both 8-bytes there. It will affect other platforms though. llvm-svn: 259575
* Fix handling of mach header and DSO handle symbols.Pete Cooper2016-02-028-40/+62
| | | | | | | | | | | | | | | | | The magic file which contained these symbols inherited from archive which meant that the resolver didn't add the required atoms as archive members only get added when referenced. Instead we now inherit from SimpleFile which always links in the atoms needed. The second issue was in the handling of these symbols when we emit the MachO. The mach header symbol needs to be in the atom list as it gets an offset (0), and being in the atom list makes sure it is emitted to the symbol table. DSO handles are not emitted to the symbol table. rdar://problem/24450654 llvm-svn: 259574
* AMDGPU: Do not promote allocas with non-inbounds GEPsMatt Arsenault2016-02-026-76/+111
| | | | | | | | If we can't assume the pointer value isn't within the bounds of the object, it seems risky to try to replace the pointer calculations. llvm-svn: 259573
* Re-submit ELF: Report multiple errors from the driver.Rui Ueyama2016-02-028-47/+78
| | | | | | This reverts r259395 which reverted r259143. llvm-svn: 259572
* ELF: Rewrite "echo" command arguments in hope that would fix a test breakage.Rui Ueyama2016-02-024-19/+19
| | | | | | | | | | | Previously, we used both single quotes and double quotes, and some single-quoted tokens are concatenated with next tokens because there were no spaces between them. That may be a cause of test flakiness on Windows, which is reported as https://llvm.org/bugs/show_bug.cgi?id=26388. The new test commands are more straightforward than before. llvm-svn: 259559
* AMDGPU: Handle promoting memmoveMatt Arsenault2016-02-022-0/+89
| | | | | | Also add missing tests for the others. llvm-svn: 259558
* ELF: Do not use fatal in LinkerScript.cpp.Rui Ueyama2016-02-022-22/+101
| | | | | | | | | | | | This patch adds "Error" field to LinkerScript class. That field is false by default, and set to true if there is a syntax error in an input file. The linker script parser is a recursive-descedent parser. Each function returns if Error is true -- so that eventually the whole parser returns to a caller. http://reviews.llvm.org/D16667 llvm-svn: 259557
* Revert "[NFC] Cleanup RangeMap.h"Todd Fiala2016-02-022-583/+1382
| | | | | | | This reverts commit r259538. Caused 92 test failures on the OS X testbot. llvm-svn: 259556
* Do not use filename in a lit test.Rui Ueyama2016-02-021-7/+7
| | | | | | So that the file is move-safe. llvm-svn: 259555
* ELF: Use StringRef instead of std::string.Rui Ueyama2016-02-021-1/+1
| | | | | | | | All MemoryBuffers for archive files are guaranteed to exist as long as their children are used in the linker. So we don't need to copy strings here. Thanks to Sean Silva for pointing this out. llvm-svn: 259554
* [X86] Fix the merging of SP updates in prologue/epilogue insertions.Quentin Colombet2016-02-022-2/+39
| | | | | | | | | When the merging was involving LEAs, we were taking the wrong immediate from the list of operands. rdar://problem/24446069 llvm-svn: 259553
* MachineVerifier: Check that defs/uses are live in subregisters as well.Matthias Braun2016-02-021-52/+141
| | | | llvm-svn: 259552
* AMDGPU: Skip promote alloca with no optimizationsMatt Arsenault2016-02-023-2/+40
| | | | llvm-svn: 259551
* AMDGPU: Minor cleanups for AMDGPUPromoteAllocaMatt Arsenault2016-02-021-27/+21
| | | | | | Mostly convert to use range loops. llvm-svn: 259550
* [Orc] Turn OrcX86_64::IndirectStubsInfo into a template helper class:Lang Hames2016-02-022-44/+46
| | | | | | | | | GenericIndirectStubsInfo. This will allow architecture support classes for other architectures to re-use this code. llvm-svn: 259549
* [codeview] Correctly handle inlining functions post-dominated by unreachableDavid Majnemer2016-02-0213-28/+154
| | | | | | | | | | | | | | CodeView requires us to accurately describe the extent of the inlined code. We did this by grabbing the next debug location in source order and using *that* to denote where we stopped inlining. However, this is not sufficient or correct in instances where there is no next debug location or the next debug location belongs to the start of another function. To get this correct, use the end symbol of the function to denote the last possible place the inlining could have stopped at. llvm-svn: 259548
* AMDGPU: Report AMDGPUPromoteAlloca changed the functionMatt Arsenault2016-02-021-22/+21
| | | | llvm-svn: 259547
* AMDGPU: Whitelist handled intrinsicsMatt Arsenault2016-02-022-8/+60
| | | | | | | We shouldn't crash on unhandled intrinsics. Also simplify failure handling in loop. llvm-svn: 259546
* AMDGPU: Use inbounds when calculating workitem offsetMatt Arsenault2016-02-022-9/+23
| | | | | | | | | | | | | When promoting allocas to LDS, we know we are indexing into a specific area just created, and the calculation will also never overflow. Also emit some of the muls as nsw nuw, because instcombine infers this already from the range metadata. I think putting this on the other adds and muls might be OK too, but I'm not 100% sure. llvm-svn: 259545
* Reverting r259529 (Marking the mmap_stress.cc TSan test as unsupported on OS X)Kuba Brecka2016-02-021-4/+0
| | | | llvm-svn: 259544
* Re-write many skip decorators to use shared code.Zachary Turner2016-02-021-205/+90
| | | | | | | | | | | | | This should be no functional change, just a refactoring of the skip decorators to all centralize on a single function, `skipTestIfFn` that does all the logic. This allows easier maintenance of the decorators and also centralizes all the hard-to-understand logic in one place. Reviewed by: Pavel Labath Differential Revision: http://reviews.llvm.org/D16741 llvm-svn: 259543
* Re-commit r259512: [tsan] Add a libc++ and lit testsuite for each ↵Daniel Sanders2016-02-024-13/+44
| | | | | | | | | | | | | | | | | | | | | | | | | | | | ${TSAN_SUPPORTED_ARCH}. Summary: This is a workaround to a problem in the 3.8 release that affects MIPS and possibly other targets where the default is not supported but a sibling is supported. When TSAN_SUPPORTED_ARCH is not empty, cmake currently attempts to build a tsan'd libcxx as well as test tsan for the default target regardless of whether the default target is supported or not. This causes problems on MIPS32 since tsan is supported for MIPS64 but not MIPS32. This patch causes cmake to only build the libcxx and run the lit test-suite for archictures in ${TSAN_SUPPORTED_ARCH} This re-commit fixes an issue where 'check-tsan' continued to look for the tsan'd libc++ in the directory it used to be built in. Reviewers: hans, samsonov Subscribers: tberghammer, llvm-commits, danalbert, srhines, dvyukov Differential Revision: http://reviews.llvm.org/D16685 llvm-svn: 259542
* Cast the fifth arg to mremap to void *Alexey Samsonov2016-02-021-1/+1
| | | | | | | | | | | | | | | | | | | | | | Summary: Since the prototype of mremap is ``` void *mremap(void *old_address, size_t old_size, size_t new_size, int flags, ... /* void *new_address*/); ``` we need to cast new_address to void * when calling mremap. Otherwise, the wrong value will be passed to mremap on x32. Patch by H.J Lu! Reviewers: kcc, eugenis, samsonov Subscribers: samsonov, llvm-commits Differential Revision: http://reviews.llvm.org/D16805 llvm-svn: 259540
* Fix Clang-tidy readability-redundant-control-flow warnings; other minor fixes.Eugene Zelenko2016-02-0217-72/+44
| | | | | | Differential revision: http://reviews.llvm.org/D16793 llvm-svn: 259539
* [NFC] Cleanup RangeMap.hTamas Berghammer2016-02-022-1382/+583
| | | | | | | | | | | | | | | | | The file contained very similar 4 implementation of the same data structure with a lot of duplicated code and some minor API differences. This CL refactor the class to eliminate the duplicated codes and to unify the APIs. RangeMap.h also contained a class called AddressDataArray what have very little added functionality over an std::vector and used only by ObjectFileMacO The CL moves the class to ObjectFileMachO.cpp as it isn't belongs into RangeMap.h and shouldn't be used in new places anyway because of the little added functionality. Differential revision: http://reviews.llvm.org/D16769 llvm-svn: 259538
* ARM: allow both vfma and vfms intrinsics on v7.Tim Northover2016-02-022-2/+17
| | | | | | | | | | | | | | The main purpose here is that vfma/vfms should be symmetric, and they are supported on most v7 cores. The new ArchGuard is suggested by ACLE but prophylactic for us. Almost all CPUs with NEON *will* have vfma, and the few exceptions I know of (e.g. Cortex-A8) are incorrectly modelled by Clang so can't trigger a test. Fortunately, they're getting rarer. But if we ever do support them properly arm_neon.h should now do the right thing. llvm-svn: 259537
* [codeview] Wire up the .cv_inline_linetable directiveReid Kleckner2016-02-0221-118/+410
| | | | | | | | This directive emits the binary annotations that describe line and code deltas in inlined call sites. Single-stepping through inlined frames in windbg now works. llvm-svn: 259535
* PR23057: Fix assertion `Val && "isa<> used on a null pointer"' on invalid ↵Denis Zobnin2016-02-024-1/+28
| | | | | | | | | | | for-range expression. Fix the issue discovered by fuzzing (PR23057, comment 18) by handling nullptr in Sema::ActOnCXXForRangeDecl and correct delayed typos in for-range expression before calling Sema::ActOnCXXForRangeStmt. Also fixes PR26288. Differential Revision: http://reviews.llvm.org/D16630 llvm-svn: 259532
* [clang-tidy] Removed unnecessary parameters in the testAlexander Kornienko2016-02-021-1/+1
| | | | llvm-svn: 259531
* [clang-tidy] Add non-constant references in function parameters check.Alexander Kornienko2016-02-027-0/+306
| | | | | | | | | | | | | | | Summary: This is implemented originally by Alexander Kornienko. Reviewers: alexfh Subscribers: cfe-commits Patch by Haojian Wu! Differential Revision: http://reviews.llvm.org/D16717 llvm-svn: 259530
* Marking the mmap_stress.cc TSan test as unsupported on OS X (it's flaky here).Kuba Brecka2016-02-021-0/+4
| | | | llvm-svn: 259529
* [MC] Enable eip-relative addressing on x86-64 for X32 ABIDerek Schuff2016-02-022-1/+40
| | | | | | | | | | | | | | | | | Summary: Enables eip-based addressing, e.g., lea constant(%eip), %rax lea constant(%eip), %eax in MC, (used for the x32 ABI). EIP-base addressing is also valid in x86_64, it is left enabled for that architecture as well. Patch by João Porto Differential Revision: http://reviews.llvm.org/D16581 llvm-svn: 259528
* XFAIL TestConsecutiveBreakpoints.test_single_step_thread_specific on OSXPavel Labath2016-02-021-0/+1
| | | | llvm-svn: 259527
* skip TestWatchLocation on OS XTodd Fiala2016-02-021-0/+1
| | | | | | | | Skipping this test while I investigate. It started failing with r259379. (It is generating an error due to unicode decode issues.) llvm-svn: 259526
* ScopInfo: Split memory access construction into different casesTobias Grosser2016-02-022-19/+104
| | | | | | | | | We create separate functions for fixed-size multi-dimensional, parameteric-sized multi-dimensional, as well as single-dimensional memory accesses to reduce the complexity of a large monolithic function. Suggested-by: Michael Kruse <llvm@meinersbur.de> llvm-svn: 259522
* ScopInfo: Do not track element-size as additional array size dimension [NFC]Tobias Grosser2016-02-022-17/+21
| | | | | | | | There is no need to pass the size of the elements as the last size dimension to ScopArrayInfo. This information is already available through the ElementType. Tracking it twice is not only redundant but may result in inconsistencies. llvm-svn: 259521
* Revert r259512 - [tsan] Add a libc++ and lit testsuite for each ↵Daniel Sanders2016-02-024-42/+12
| | | | | | | | | ${TSAN_SUPPORTED_ARCH}. check-tsan does not pick up the correct libc++.so. It succeeded on my machine by picking up the libc++.so that was built before making this change. llvm-svn: 259519
* Make CodeGen headers self-contained.Benjamin Kramer2016-02-021-1/+1
| | | | llvm-svn: 259518
* Remove redundant test in TestExitDuringStepPavel Labath2016-02-021-12/+4
| | | | | | | | | After recent changes, test_thread_state_is_stopped has become equivalent to test_step_in, as the function exit_during_step_base was not using the "test_thread_state" parameter. As test was XFAILed on all platforms anyway, and we have other tests for the bug which it (used to) test, I am simply removing the function. llvm-svn: 259517
* Expand comment a bit.Rafael Espindola2016-02-021-0/+5
| | | | | | | I have spent some time prototyping this idea. While it seems to work, I now think it is probably not worth it. llvm-svn: 259516
* [AArch64] Add a FIXME comment.Chad Rosier2016-02-021-0/+2
| | | | llvm-svn: 259515
* Log error message in SBTarget::LaunchPavel Labath2016-02-021-3/+2
| | | | llvm-svn: 259514
* Mark TestProcessIO.test_stdin_redirection as flaky on androidPavel Labath2016-02-021-0/+1
| | | | | | bug #26437 llvm-svn: 259513
* [tsan] Add a libc++ and lit testsuite for each ${TSAN_SUPPORTED_ARCH}.Daniel Sanders2016-02-024-12/+42
| | | | | | | | | | | | | | | | | | | | | | | Summary: This is a workaround to a problem in the 3.8 release that affects MIPS and possibly other targets where the default is not supported but a sibling is supported. When TSAN_SUPPORTED_ARCH is not empty, cmake currently attempts to build a tsan'd libcxx as well as test tsan for the default target regardless of whether the default target is supported or not. This causes problems on MIPS32 since tsan is supported for MIPS64 but not MIPS32. This patch causes cmake to only build the libcxx and run the lit test-suite for archictures in ${TSAN_SUPPORTED_ARCH} Reviewers: hans, samsonov Subscribers: tberghammer, llvm-commits, danalbert, srhines, dvyukov Differential Revision: http://reviews.llvm.org/D16685 llvm-svn: 259512
* [WWW] Add our Polly/OpenCL paperJohannes Doerfert2016-02-021-0/+7
| | | | llvm-svn: 259511
* [AArch64] Allocate the modified and used regs only once per function.Chad Rosier2016-02-021-12/+17
| | | | llvm-svn: 259510
* Fix single stepping over the IT instructionTamas Berghammer2016-02-021-5/+16
| | | | | | | | | | | | | | | | | The ARM instruction emulator had 2 bugs related to the handling of the IT instruction causing an error in single stepping: * We haven't initialized the IT mask from the CPSR so if the last instruction of the IT block is a branch and the condition is false then the emulator evaluated the branch what resulted in an incorrect pc for the next instruction. * The ITSTATE was advanced before the execution of each instruction. As a result the emulator was using the condition of following instruction in every case. The ITSTATE should be edvanced after the execution of an instruction except after an IT instruction. Differential revision: http://reviews.llvm.org/D16772 llvm-svn: 259509
* WebAssembly: update expected GCC torture test failuresJF Bastien2016-02-021-3/+0
| | | | | | The 3 programs used __attribute__((mode(?))) on enum, which clang r259497 fixed. llvm-svn: 259508
* Make the remaining headers self-contained.Benjamin Kramer2016-02-0211-11/+14
| | | | llvm-svn: 259507
OpenPOWER on IntegriCloud