| 09df2b066221d869f17f4b5762405f111a65f983 |
|
16-Jul-2013 |
Tim Northover <tnorthover@apple.com> |
ARM: implement low-level intrinsics for the atomic exclusive operations.
This adds three overloaded intrinsics to Clang:
T __builtin_arm_ldrex(const volatile T *addr)
int __builtin_arm_strex(T val, volatile T *addr)
void __builtin_arm_clrex()
The intent is that these do what users would expect when given most sensible
types. Currently, "sensible" translates to ints, floats and pointers.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@186394 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| ad24ad4c741cad0fe79d6e4a74edc58d592a0f90 |
|
13-Jun-2013 |
Rafael Espindola <rafael.espindola@gmail.com> |
Allow clang to build __clear_cache on ARM.
__clear_cache is special. It needs no signature, but is a real function in
compiler_rt or libgcc.
Patch by Andrew Turner.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@183926 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 173a4cc51a416a938885358b9592e629728e7407 |
|
14-May-2013 |
Rafael Espindola <rafael.espindola@gmail.com> |
Really fix the declaration of __clear_cache.
When I tested gcc's behaviour before, I forgot the extern "C", so it
would warn when the types *did* match.
So in the end
* __clear_cache takes two void pointers.
* aarch64 was correct before.
* libgcc's manual is wrong.
* this patch fixes arm.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@181810 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 4537d6e0f9baf2e011a4260e0d7872789b01c3f2 |
|
14-May-2013 |
Rafael Espindola <rafael.espindola@gmail.com> |
Fix __clear_cache on ARM.
Current gcc's produce an error if __clear_cache is anything but
__clear_cache(char *a, char *b);
It looks like we had just implemented a gcc bug that is now fixed.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@181784 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 26c1b8df8d1af0d8ef7f6c726fe1a8a9ddc60267 |
|
28-May-2011 |
Bruno Cardoso Lopes <bruno.cardoso@gmail.com> |
Add support for ARM ldrexd/strexd builtins
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@132249 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 2bc0e5d955dbee5518afa59e1c66025a78b097f1 |
|
03-May-2011 |
Bruno Cardoso Lopes <bruno.cardoso@gmail.com> |
Add a few ARM coprocessor builtins. The llvm side of the commit contains the intrinsics and matching patterns.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@130765 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 99c40bb13b523d58d7aeb6446e4f486d6918ca58 |
|
03-Aug-2010 |
Nate Begeman <natebegeman@mac.com> |
Add support for VFP status & control operations for ARM.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@110153 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| bb37f50c2d0d72e1fa5b349d5f6a11fdc5acb86e |
|
30-Jul-2010 |
Nate Begeman <natebegeman@mac.com> |
Wire up sema checking for __builtin_arm_usat and __builtin_arm_ssat immediates.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@109814 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| f6404774069a4759cab095b389ce007e74c9c9ee |
|
29-Jul-2010 |
Nate Begeman <natebegeman@mac.com> |
Add codegen support for ARM qadd & qsub intrinsics
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@109771 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 1058253c364b2c98e6cecfe15d18d3562db245f4 |
|
16-Jul-2010 |
Daniel Dunbar <daniel@zuster.org> |
Builtins/ARM: __clear_cache doesn't seem to have a consistent prototype, declare
the builtin as void __clear_cache(...) to workaround this, which appears to
match what GCC does.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@108487 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| a23326b5c244a03bf61ebb86db60a777ea26f926 |
|
17-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
Generate arm_neon.inc in include/clang/Basic, which provides:
1. builtins definitions for BuiltinsARM.def
2. intrinsic validation code for SemaChecking
Unsure as to whether this is the best way to handle the make dependencies or not.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@106208 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| cba9421f5c9f784bd32fcddf55b6af4b6e024904 |
|
12-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
vbsl, vrev* is implemented via arm_neon.h
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105875 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| d075c01c359b9cc120c3accc7166990f9f4ac423 |
|
10-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
support _lane ops, and multiplies by scalar.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105770 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| df98e1d1da5ab1ca7c325378fc1c2eaa90a6476d |
|
09-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
Implement codegen for hadd, hsub, max, min, mlal, movl, movn, padal, mov_n
Make note about how to handle the dozen or so multiply by scalar ops.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105734 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 95450f6ffc89ee218faa550433265f80930469c4 |
|
09-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
More accurate BuiltinsARM.def
vget_lane support
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105684 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 1c2a88cfaeb11227d3a6bf7204207e0c8cf6de6f |
|
09-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
Implement transpose/zip/unzip & table lookup.
Test out some basic constant-checking.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105667 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 30d91718a676177f0d0d0210ce4fdb4f616df6e5 |
|
08-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
Fix NEON intrinsic argument passing, support vext. Most now successfully make it through codegen to the .s file
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105599 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 9eb65a56e18bee1e5392bf2dff01cbd7b895f685 |
|
08-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
Implement ARM NEON up through vcvt, alphabetically.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105590 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 79ba509b0106fd0a1ff832baeb1fdb5430527efe |
|
07-Jun-2010 |
Rafael Espindola <rafael.espindola@gmail.com> |
Implement __clear_cache on ARM.
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105537 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| aa1381ba9b5251a40975e262b36e6a98ec19c3b4 |
|
04-Jun-2010 |
Nate Begeman <natebegeman@mac.com> |
Initial support for ARM NEON builtins, codegen up next
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@105489 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|
| 2752c0137d95aa2f4ee1cdff4b564bac842e041b |
|
03-Mar-2010 |
Chris Lattner <sabre@nondot.org> |
add framework for ARM builtins, Patch by Edmund Grimley Evans!
git-svn-id: https://llvm.org/svn/llvm-project/cfe/trunk@97656 91177308-0d34-0410-b5e6-96231b3b80d8
/external/clang/include/clang/Basic/BuiltinsARM.def
|