shylie/llvm-project
1
0
Fork 0
Code Issues Pull Requests Actions 6 Packages Projects Releases Wiki Activity
97,504 Commits 1,713 Branches 298 Tags
Commit Graph

2074 Commits

Author SHA1 Message Date
Bill Wendling
73a48d83b2 Get rid of ellipses. 
llvm-svn: 121589
 2010-12-10 22:54:30 +00:00
Jim Grosbach
e119da1146 Thumb unconditional branch binary encoding. rdar://8754994 
llvm-svn: 121496
 2010-12-10 18:21:33 +00:00
Jim Grosbach
78485ad65e Thumb conditional branch binary encodings. rdar://8745367 
llvm-svn: 121493
 2010-12-10 17:13:40 +00:00
Bob Wilson
4959014850 The Neon vqdmlsl_lane and vqdmlal_lane intrinsics have 4 arguments, not 3. 
llvm-svn: 121469
 2010-12-10 06:37:53 +00:00
Jim Grosbach
529c7e8d1f Thumb needs a few different encoding schemes for branch targets. Rename 
t_brtarget to be more specific.

llvm-svn: 121398
 2010-12-09 19:01:46 +00:00
Bob Wilson
47206b840b 80-column fixes. 
llvm-svn: 121395
 2010-12-09 18:43:35 +00:00
Bob Wilson
38c3ca78e6 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
Michael J. Spencer
7b6fef82d4 Support/MemoryBuffer: Replace all uses of std::string *ErrMsg with error_code &ec. And fix clients. 
llvm-svn: 121379
 2010-12-09 17:36:48 +00:00
Bill Wendling
3392bfc8f3 The BLX instruction is encoded differently than the BL, because why not? In 
particular, the immediate has 20-bits of value instead of 21. And bit 0 is '0'
always. Going through the BL fixup encoding was trashing the "bit 0 is '0'"
invariant.

Attempt to get the encoding at slightly more correct with this.

llvm-svn: 121336
 2010-12-09 00:39:08 +00:00
Bill Wendling
a7d6aa902a Support the "target" encodings for the CB[N]Z instructions. 
llvm-svn: 121308
 2010-12-08 23:01:43 +00:00
Bob Wilson
4868ba0619 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
dbe9e7e3dd 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
bf74755e62 Remove unused function parameter. 
llvm-svn: 121286
 2010-12-08 21:39:00 +00:00
Bob Wilson
194ad82666 Add an operator for vaba so it can be implemented using vabd. 
llvm-svn: 121276
 2010-12-08 20:09:10 +00:00
Bill Wendling
55bc7187ac Use this new fangled StringSwitch technology. 
llvm-svn: 121273
 2010-12-08 20:02:49 +00:00
Bill Wendling
4182a16930 Cleanup table a bit. 
llvm-svn: 121250
 2010-12-08 13:03:15 +00:00
Bill Wendling
8a6449c46e Add support for loading from a constant pool. 
llvm-svn: 121226
 2010-12-08 01:57:09 +00:00
Bob Wilson
97b44b5b4a 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
c40935fa0c 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
7a36c68748 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
Jim Grosbach
fb116aed60 Add source Record* reference to PatternToMatch. Allows better diagnostics. 
llvm-svn: 121196
 2010-12-07 23:05:49 +00:00
Bob Wilson
361afe4ef2 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
17a233c0e5 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
Jim Grosbach
f878e62a0d Remove reference to the CMPz instruction patterns for ARM. 
llvm-svn: 121180
 2010-12-07 20:44:33 +00:00
Bob Wilson
192336b865 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
Jim Grosbach
8656d82b5b Trailing whitespace. 
llvm-svn: 121167
 2010-12-07 19:36:07 +00:00
Jim Grosbach
e99956eb3e Change assert to diagnostic. Message still needs work, but it's better than 
an assert, at least.

llvm-svn: 121166
 2010-12-07 19:35:36 +00:00
Bob Wilson
654db47903 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
b87116e30a Fix whitespace. 
llvm-svn: 121086
 2010-12-07 01:12:19 +00:00
Jim Grosbach
9e1994698d Add fixup for Thumb1 BL/BLX instructions. 
llvm-svn: 121072
 2010-12-06 23:57:07 +00:00
Bob Wilson
236ba8d862 Remove trailing whitespace. 
llvm-svn: 120891
 2010-12-04 04:40:15 +00:00
Bob Wilson
074436b090 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
Bill Wendling
4e7eb12f6f I did it wrong. Don't disregard these encodings here. 
llvm-svn: 120786
 2010-12-03 02:25:59 +00:00
Bill Wendling
e38f1149fa Ignore decode table conflicts in the tMOVgpr2tgpr, tMOVgpr2gpr, and tMOVtgpr2gpr 
instructions. They are handled as special moves, but encoded as a normal move.

llvm-svn: 120779
 2010-12-03 01:55:30 +00:00
Bob Wilson
e6b421ccb5 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
791934e122 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
4375586bd9 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
79026235e6 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
014fe01ac8 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
492de6da40 Add casts for splatted scalars in calls to Neon builtins. 
llvm-svn: 120641
 2010-12-02 01:18:23 +00:00
Bob Wilson
ec626b09cb 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
c08944fd5a Add another missing cast for Neon vcombine results. 
llvm-svn: 120639
 2010-12-02 01:18:18 +00:00
Bob Wilson
a9ea9ef840 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
743eeae937 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
be764f0cd1 Cast scalar results of Neon macros to the correct type. 
llvm-svn: 120631
 2010-12-02 00:24:56 +00:00
Bob Wilson
3e8f3f94ef 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
fa5207595e Add some comments for TableGen's NeonEmitter. 
llvm-svn: 120596
 2010-12-01 19:49:56 +00:00
Bob Wilson
65a96d082a Cleanup: simplify checks for integers between 2 and 4. 
llvm-svn: 120595
 2010-12-01 19:49:51 +00:00
Jim Grosbach
dc35e067c1 Refactor LEApcrelJT as a pseudo-instructionlowered to a cannonical ADR 
instruction at MC lowering. Add binary encoding information for the ADR,
including fixup data for the label operand.

llvm-svn: 120594
 2010-12-01 19:47:31 +00:00
Owen Anderson
8335e8fa63 Simplify the encoding of reg+/-imm12 values that allow PC-relative encoding. This allows the 
Thumb2 encoding to share code with the ARM encoding, which gets use fixup support for free.
It also allows us to fold away at least one codegen-only pattern.

llvm-svn: 120481
 2010-11-30 22:45:47 +00:00