RPCS3/archived-llvm-mirror
1
0
Fork 0
mirror of https://github.com/RPCS3/llvm-mirror.git synced 2026-01-31 01:35:20 +01:00
Code Issues Packages Projects Releases Wiki Activity
69,890 Commits 6 Branches 7 Tags
4e7ec00a1dd1feef48b855024bfb376143b5872d
Commit Graph

84 Commits

Author SHA1 Message Date
Bob Wilson
4e879f0f00 Use __builtin_shufflevector to implement vget_low and vget_high intrinsics. 
This was suggested by Edmund Grimley Evans in pr8411.

llvm-svn: 123043
 2011-01-07 23:40:49 +00:00
Bob Wilson
8d93d7b4fd Neon intrinsic tests need to be compiled for Cortex-A9 for f16 support. 
llvm-svn: 122015
 2010-12-17 01:21:03 +00:00
Bob Wilson
7e64a19960 Teach the Neon intrinsic generator to widen half-precision float types. 
This isn't currently used for anything but I ran into it when experimenting
with some changes, and it might be useful in the future.

llvm-svn: 121911
 2010-12-15 23:16:25 +00:00
Bob Wilson
3e4aa8ec69 Add a Neon intrinsic test generator. 
This is still a WIP.  It's already good enough to expose a few bugs, though.

llvm-svn: 121868
 2010-12-15 16:58:45 +00:00
Bob Wilson
114df2f88a Fix Neon intrinsic immediate range checking for some double-register operands. 
Some quad-register intrinsics with lane operands only take a double-register
operand for the vector containing the lane.  The valid range of lane numbers
is then half as big as you would expect from the quad-register type.
Note: This currently has no effect because those intrinsics are now handled
entirely in the header file using __builtin_shufflevector, which does its own
range checking, but I want to use this for generating tests.

llvm-svn: 121867
 2010-12-15 16:58:42 +00:00
Bob Wilson
f99cd09e3f The Neon vqdmlsl_lane and vqdmlal_lane intrinsics have 4 arguments, not 3. 
llvm-svn: 121469
 2010-12-10 06:37:53 +00:00
Bob Wilson
3c35e2ab2f 80-column fixes. 
llvm-svn: 121395
 2010-12-09 18:43:35 +00:00
Bob Wilson
bd5b0c9ec6 Add a license comment to the generated arm_neon.h header. 
Remove the previous header.  I don't think we need to expose to end users
that we use TableGen to produce our version of arm_neon.h, and that header
was also using doubleslash comments which could be a problem when using it
in strict C89 compilations.

llvm-svn: 121390
 2010-12-09 18:31:01 +00:00
Bob Wilson
8c693a934a Add operators for "_lane" variants of some saturating Neon multiply intrinsics 
so they can be implemented without separate clang builtins.

llvm-svn: 121299
 2010-12-08 22:36:08 +00:00
Bob Wilson
b258f6e80b Add operators for vabdl and vabal so they can be implemented without builtins. 
llvm-svn: 121287
 2010-12-08 21:39:04 +00:00
Bob Wilson
368438b3ac Remove unused function parameter. 
llvm-svn: 121286
 2010-12-08 21:39:00 +00:00
Bob Wilson
9cb69260e2 Add an operator for vaba so it can be implemented using vabd. 
llvm-svn: 121276
 2010-12-08 20:09:10 +00:00
Bob Wilson
dd1d9cf3b6 Add operators for vadd[lw] and vsub[lw] 
so they can be implemented without clang builtins.

llvm-svn: 121213
 2010-12-08 00:14:04 +00:00
Bob Wilson
937fe73ee2 Add operators for vmlal{_n,_lane} and vmlsl{_n,_lane} 
so they can be implemented without clang builtins.

llvm-svn: 121209
 2010-12-07 23:53:37 +00:00
Bob Wilson
8182bc40cd Emit vmovl intrinsics first in the arm_neon.h header 
so they can be used in the implementations of other intrinsics.

llvm-svn: 121208
 2010-12-07 23:53:32 +00:00
Bob Wilson
93b8add7dd Add an operator for vdup_lane so it can be implemented without a clang builtin. 
llvm-svn: 121190
 2010-12-07 22:39:24 +00:00
Bob Wilson
9d8115889c Add an operator for vmull_lane so it can be implemented without a clang builtin. 
llvm-svn: 121187
 2010-12-07 22:02:48 +00:00
Bob Wilson
8079f3377d Add new built-in operations for vmull and vmull_n 
so they can be implemented without requiring clang builtins.
Radar 8446238.

llvm-svn: 121173
 2010-12-07 20:02:45 +00:00
Bob Wilson
f909f96f2b Add an OpReinterpret operation to TableGen's NeonEmitter. 
An OpReinterpret entry is handled by translating it to OpCast intrinsics for
all combinations of source and destination types with the same total size.
This will be used to generate all the vreinterpret intrinsics.

llvm-svn: 121087
 2010-12-07 01:12:23 +00:00
Bob Wilson
6492963708 Fix whitespace. 
llvm-svn: 121086
 2010-12-07 01:12:19 +00:00
Bob Wilson
5917f1a762 Remove trailing whitespace. 
llvm-svn: 120891
 2010-12-04 04:40:15 +00:00
Bob Wilson
8015024bdf Get Neon intrinsic names from the new "Name" field in the tblgen records 
instead of just converting the record name to lowercase.

llvm-svn: 120809
 2010-12-03 17:19:39 +00:00
Bob Wilson
2e2ccbe986 Add support for "_lane" variants of VMUL, VMLA, and VMLS Neon intrinsics. 
llvm-svn: 120764
 2010-12-03 00:34:12 +00:00
Bob Wilson
73a62b36c6 Support using macros for Neon intrinsics implemented without builtins. 
Intrinsics implemented with Clang builtins could already be implemented as
either inline functions or macros, but intrinsics implemented directly
(without builtins) could only be inline functions.

llvm-svn: 120763
 2010-12-03 00:34:09 +00:00
Bob Wilson
a6ebc72f34 Simplify code in Neon intrinsics. No functional changes intended. 
For most intrinsics, there is no need to allocate a temporary to hold the
result value; just return it directly.

llvm-svn: 120695
 2010-12-02 07:44:23 +00:00
Bob Wilson
1410cd5668 Assign arguments of Neon intrinsic macros to local temporaries. 
Since we're casting them for the calls to the builtins, we need this to
make sure their types get checked in the same way they would if the intrinsics
were implemented as inline functions.

llvm-svn: 120693
 2010-12-02 07:10:39 +00:00
Bob Wilson
1beac04144 Use statement expressions in Neon intrinsics defined as macros. 
This is in preparation for adding assignments to temporaries to ensure
that the proper type checking is done.

llvm-svn: 120649
 2010-12-02 02:42:51 +00:00
Bob Wilson
59b1977d0a Add casts for splatted scalars in calls to Neon builtins. 
llvm-svn: 120641
 2010-12-02 01:18:23 +00:00
Bob Wilson
7680d2f36a Add a missing cast for Neon vsbl results. 
The bitwise operations are always done with unsigned values, but the result may
be signed.

llvm-svn: 120640
 2010-12-02 01:18:20 +00:00
Bob Wilson
c7d49b591c Add another missing cast for Neon vcombine results. 
llvm-svn: 120639
 2010-12-02 01:18:18 +00:00
Bob Wilson
f01547ed73 Add casts in arm_neon.h for result values in inline functions as well as macros. 
We should not rely on lax-vector-conversions for these intrinsics to work.

llvm-svn: 120638
 2010-12-02 01:18:15 +00:00
Bob Wilson
d28c6da501 Avoid "char" for Neon vector elements; make it explicitly signed (or unsigned). 
llvm-svn: 120632
 2010-12-02 00:24:59 +00:00
Bob Wilson
b475c5a1ff Cast scalar results of Neon macros to the correct type. 
llvm-svn: 120631
 2010-12-02 00:24:56 +00:00
Bob Wilson
b3f9b6c2d5 Add explicit casts for vector arguments to Neon builtins. 
This avoids warnings with -Wvector-conversions.  Radar 8228022.

llvm-svn: 120597
 2010-12-01 19:49:58 +00:00
Bob Wilson
b2affb91cd Add some comments for TableGen's NeonEmitter. 
llvm-svn: 120596
 2010-12-01 19:49:56 +00:00
Bob Wilson
84b6b4c00e Cleanup: simplify checks for integers between 2 and 4. 
llvm-svn: 120595
 2010-12-01 19:49:51 +00:00
Bob Wilson
77071bcf8a Fix copy-and-paste error in exception message. 
llvm-svn: 120033
 2010-11-23 19:38:34 +00:00
Bob Wilson
a9561a6257 Change the 'x' type modifier for Neon intrinsics to force a signed integer. 
This makes it symmetric with the 'u' modifier that forces an unsigned type.
This is needed for unsigned vector shifts, where the shift amount still needs
to be signed.  PR8482 (Radar 8603521).

llvm-svn: 119742
 2010-11-18 21:43:22 +00:00
Bob Wilson
2f7de3aad6 Use new neon_vector_type and neon_polyvector_type attributes for Neon vectors. 
llvm-svn: 119406
 2010-11-16 23:57:06 +00:00
Bob Wilson
b48fd4816a Change Neon polynomial types to be signed to match GCC. 
llvm-svn: 119405
 2010-11-16 23:57:03 +00:00
Bob Wilson
f2bb931c9f Refactor to new GetNumElements function. 
No functional change.

llvm-svn: 119404
 2010-11-16 23:57:01 +00:00
Bob Wilson
efff1285d2 Tidy up some things in <arm_neon.h>. 
Stop defining types with "__neon_" prefixes and then using typedefs without
the prefix; there's no reason to do that anymore.  Remove types that combine
multiple Neon vectors and treat them as a single long vector; they are not
used.

llvm-svn: 119369
 2010-11-16 19:39:14 +00:00
Bob Wilson
808941eb3b Reapply "Stop using struct wrappers for Neon vector types in <arm_neon.h>." 
I've temporarily disabled the failing clang test.

llvm-svn: 119367
 2010-11-16 19:16:06 +00:00
Bob Wilson
e1e6afe51b Revert "Stop using struct wrappers for Neon vector types in <arm_neon.h>." 
It's breaking buildbots.

llvm-svn: 119363
 2010-11-16 18:43:07 +00:00
Bob Wilson
c33bc803b5 Stop using struct wrappers for Neon vector types in <arm_neon.h>. 
Thanks to Nate Begeman for an earlier version of this patch.

llvm-svn: 119358
 2010-11-16 18:17:03 +00:00
Nate Begeman
6af7c7163f Revert r114596, it's breaking a few tests. 
llvm-svn: 114659
 2010-09-23 16:49:17 +00:00
Nate Begeman
98c68ffb0c <rdar://problem/8228022> Wvector-conversions warnings in arm_neon.h 
Explicitly cast arguments to the type the builtin expects, which is <vN x i8>

llvm-svn: 114596
 2010-09-22 22:28:42 +00:00
Bob Wilson
57c4ffb2f3 Use float64 instead of int64 vector elements for NEON vget_low and vget_high 
functions, since int64 is not a legal type and using it leads to inefficient
code.  PR8036.

llvm-svn: 113919
 2010-09-15 01:52:33 +00:00
Bob Wilson
3cef16bee1 Tidy whitespace in generated arm_neon.h. 
llvm-svn: 113865
 2010-09-14 21:52:34 +00:00
Nate Begeman
aa169cc470 Add tablegen support for vdup_lane 
llvm-svn: 110419
 2010-08-06 01:24:11 +00:00