RPCS3/llvm-mirror
1
0
Fork 0
mirror of https://github.com/RPCS3/llvm-mirror.git synced 2024-11-24 03:33:20 +01:00
Code Issues Projects Releases Wiki Activity
67,668 Commits 4 Branches 5 Tags 704 MiB
7680d2f36a
Commit Graph

56 Commits

Author SHA1 Message Date
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
Bob Wilson
c9fcc66f8e Fix a warning from gcc-4.0 (from the ppc buildbot). 
llvm-svn: 109605
 2010-07-28 18:21:10 +00:00
Bob Wilson
5ddef25de2 Change array references to match my previous change to use the public type 
names for the array fields.

llvm-svn: 106803
 2010-06-24 22:21:19 +00:00
Bob Wilson
45cb379048 Fix up some comments. 
llvm-svn: 106795
 2010-06-24 22:04:30 +00:00
Bob Wilson
f0df97699e Use the struct tags mandated by ARM's ABI. Also use the public type names for 
the array fields in these structs.

llvm-svn: 106794
 2010-06-24 22:03:41 +00:00
Nate Begeman
8a4ebbc2a6 Add support for returning multiple vectors via sret, which is how the ARM target expects the intrinsics to work. 
llvm-svn: 106406
 2010-06-20 21:09:52 +00:00
Nate Begeman
b94f5f1d97 Modify tablegen to support generating all NEON code used by clang at once. 
llvm-svn: 106207
 2010-06-17 04:15:13 +00:00
Nate Begeman
e25fc6a8e4 Make VC++ happy 
llvm-svn: 106054
 2010-06-15 22:10:31 +00:00
Nate Begeman
9d86772d50 Add the last of the SemaChecking-gen code. 
llvm-svn: 105929
 2010-06-14 05:17:23 +00:00
Nate Begeman
955d383e5b Add a helping of comments 
Add code for generating bits of semachecking

llvm-svn: 105907
 2010-06-13 04:47:03 +00:00
Chris Lattner
3fdb8fcaeb declare a class with 'class' instead of struct to avoid tag mismatch 
warnings, and don't shift by a bool.  Patch by Rizky Herucakra!

llvm-svn: 105886
 2010-06-12 15:46:56 +00:00
Nate Begeman
59394ea1ed Add generic vector support for bitselect & element byteswap 
llvm-svn: 105874
 2010-06-12 03:09:49 +00:00
Nate Begeman
7a1f1649b9 Add support for polynomial type, for polynomial multiply 
llvm-svn: 105792
 2010-06-10 18:06:07 +00:00
Nate Begeman
7b0f786883 NEON support for _lane ops, and multiplies by scalar. 
llvm-svn: 105769
 2010-06-10 00:16:56 +00:00
Nate Begeman
905696c6eb Further refine types for operations which take scalars. 
This will be used primarily by NEON shift intrinsics.

llvm-svn: 105733
 2010-06-09 18:02:26 +00:00
Nate Begeman
e0f6bd0055 Specialize I-Class instructions better so that we have less work to do in codegen. 
Parenthesize macro args

llvm-svn: 105682
 2010-06-09 05:11:55 +00:00
Nate Begeman
10b97ea32f Handle instructions which need to be #defines for the purpose of capturing constant arguments 
Handle extract hi/lo with common code

llvm-svn: 105666
 2010-06-09 01:09:00 +00:00
Nate Begeman
c470186332 Fix a valgrind error. 
llvm-svn: 105600
 2010-06-08 07:11:17 +00:00
Nate Begeman
8df074e074 Refine BuiltinsARM.def types a bit, we should do a better job of this to save some c++ code in CGBuiltins. 
llvm-svn: 105598
 2010-06-08 06:01:16 +00:00
Nate Begeman
77a2b1b8b4 ARM NEON: 
fix vcvt naming
handle vdup, vcombine with generic vector code

llvm-svn: 105588
 2010-06-08 00:14:42 +00:00
Nate Begeman
477813692f clang codegen support 
llvm-svn: 105531
 2010-06-07 16:00:37 +00:00
Nate Begeman
7a41bddd2c Handle multi-vector returns and args. 
llvm-svn: 105496
 2010-06-04 22:53:30 +00:00
Nate Begeman
60df12eda6 Additional fixes to BuiltinsARM.def generator, on to clang codegen. 
llvm-svn: 105488
 2010-06-04 21:36:00 +00:00
Nate Begeman
8275ffe1df Progress on generating BuiltinsARM.def, still some duplicates to work out. 
llvm-svn: 105461
 2010-06-04 07:11:25 +00:00
Nate Begeman
766330952e BuiltinsARM.def emitter, still needs a substantial bit of tweaking to lighten the load on clang. 
llvm-svn: 105456
 2010-06-04 01:26:15 +00:00
Nate Begeman
b5c41fee97 Mangle __builtin_neon_* names appropriately. 
Add skeleton of support for emitting the list of prototypes for BuiltinsARM.def

llvm-svn: 105443
 2010-06-04 00:21:41 +00:00
Nate Begeman
6483dc5067 Add some additional capabilities to the neon emitter 
llvm-svn: 105416
 2010-06-03 21:35:22 +00:00
Nate Begeman
86df2ed097 arm_neon.h now makes it through clang and generates appropriate code for those functions which can use 
generic vector operators rather than __builtin_neon_*

llvm-svn: 105380
 2010-06-03 04:04:09 +00:00
Nate Begeman
d0fe2c84d7 arm_neon.h emitter now mostly complete for the purposes of initial testing. 
llvm-svn: 105349
 2010-06-02 21:53:00 +00:00