RPCS3/llvm-mirror
1
0
Fork 0
mirror of https://github.com/RPCS3/llvm-mirror.git synced 2024-11-25 04:02:41 +01:00
Code Issues Projects Releases Wiki Activity
67,953 Commits 4 Branches 5 Tags 704 MiB
51082ed2a4
Commit Graph

67953 Commits

This Branch
This Branch
All Branches
Author SHA1 Message Date
Jim Grosbach
51082ed2a4 Add operand encoding for Thumb2 addw SP + imm. rdar://8745434 
llvm-svn: 121305
 2010-12-08 22:50:19 +00:00
Jim Grosbach
e1eb84a44a Parameterize opcode encoding bits for Thumb2 extended precision integer 
multiply instructions.

llvm-svn: 121301
 2010-12-08 22:38:41 +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
Jim Grosbach
13c16125f1 Fix operand encoding for Thumb2 extended precision multiplies. rdar://8745555 
llvm-svn: 121297
 2010-12-08 22:29:28 +00:00
Jakob Stoklund Olesen
3c81b6a50b Store (priority,regnum) pairs in the priority queue instead of providing an 
abstract priority queue interface in subclasses that want to override the
priority calculations.

Subclasses must provide a getPriority() implementation instead.

This approach requires less code as long as priorities are expressable as simple
floats, and it avoids the dangers of defining potentially expensive priority
comparison functions.

It also should speed up priority_queue operations since they no longer have to
chase pointers when comparing registers. This is not measurable, though.

Preferably, we shouldn't use floats to guide code generation. The use of floats
here is derived from the use of floats for spill weights. Spill weights have a
dynamic range that doesn't lend itself easily to a fixpoint implementation.

When someone invents a stable spill weight representation, it can be reused for
allocation priorities.

llvm-svn: 121294
 2010-12-08 22:22:41 +00:00
Eric Christopher
d492f798d1 Reword comment slightly. 
llvm-svn: 121293
 2010-12-08 22:21:42 +00:00
Lang Hames
334ef20886 Fixed some dependencies in RegAllocPBQP.h . Thanks to Borja Ferrer for pointing out this issue. 
llvm-svn: 121292
 2010-12-08 22:15:32 +00:00
Jim Grosbach
063c38c6df Simplify T2 operand assignment notation a bit. No need to specify a bit range 
for the source field when it's the whole thing that's being referenced.

llvm-svn: 121291
 2010-12-08 22:10:43 +00:00
Devang Patel
e515e18523 Use type's file info while describing inheritance relationship. 
llvm-svn: 121289
 2010-12-08 21:46:37 +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
Eric Christopher
77d3a7b3fb Fix comment. 
llvm-svn: 121285
 2010-12-08 21:35:09 +00:00
Jakob Stoklund Olesen
f04d283db1 Trim includes. 
llvm-svn: 121283
 2010-12-08 21:12:00 +00:00
Devang Patel
90fd70aa09 Add support to create debug info for functions and methods. 
llvm-svn: 121281
 2010-12-08 20:42:44 +00:00
Jim Grosbach
5e900612ff Tweak ARM fixup value adjustments for Thumb to better handle the half-word 
ordering of thumb mode.

llvm-svn: 121280
 2010-12-08 20:32:07 +00:00
Devang Patel
53f05af4c1 Add support to create class type. 
llvm-svn: 121279
 2010-12-08 20:18:20 +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
Andrew Trick
fb72ca2129 Generalize PostRAHazardRecognizer so it can be used in any pass for 
both forward and backward scheduling. Rename it to
ScoreboardHazardRecognizer (Scoreboard is one word). Remove integer
division from the scoreboard's critical path.

llvm-svn: 121274
 2010-12-08 20:04:29 +00:00
Bill Wendling
24e6d5a4f2 Use this new fangled StringSwitch technology. 
llvm-svn: 121273
 2010-12-08 20:02:49 +00:00
Owen Anderson
d5c17d5981 Improve comment. 
llvm-svn: 121272
 2010-12-08 19:31:11 +00:00
Jim Grosbach
16cdaf34bc Add initializer. 
llvm-svn: 121262
 2010-12-08 15:36:45 +00:00
Bill Wendling
3e1be94d7e Cleanup table a bit. 
llvm-svn: 121250
 2010-12-08 13:03:15 +00:00
Evan Cheng
5582f058f4 Add comments. 
llvm-svn: 121238
 2010-12-08 06:29:02 +00:00
Jakob Stoklund Olesen
d638b989f2 Stub out RegAllocGreedy. 
This new register allocator is initially identical to RegAllocBasic, but it will
receive all of the tricks that RegAllocBasic won't get.

RegAllocGreedy will eventually replace linear scan.

llvm-svn: 121234
 2010-12-08 03:26:16 +00:00
Bill Wendling
c5a48281fa Fix newlines. 
llvm-svn: 121233
 2010-12-08 02:46:25 +00:00
Daniel Dunbar
164cb86163 build: Shared libraries shouldn't used RPATH on Darwin, only main executables 
should use that.

llvm-svn: 121231
 2010-12-08 02:29:26 +00:00
Eric Christopher
7b87454424 Regenerate this for Daniel. 
llvm-svn: 121227
 2010-12-08 02:02:14 +00:00
Bill Wendling
dac1f24d98 Add support for loading from a constant pool. 
llvm-svn: 121226
 2010-12-08 01:57:09 +00:00
Devang Patel
b7a7988b6b Add support to create vector, array, enums etc... 
llvm-svn: 121224
 2010-12-08 01:50:15 +00:00
Daniel Dunbar
28f51a7c4a build: Don't force -flat_namespace or '-undefined suppress' on unsuspecting users of LLVM makefiles, these options really shouldn't be used on Darwin. 
llvm-svn: 121223
 2010-12-08 01:48:05 +00:00
Daniel Dunbar
32c68a7d29 autoconf: Stop lying to me. 
llvm-svn: 121222
 2010-12-08 01:48:03 +00:00
Jim Grosbach
d4eea7c10d Let target asm backends see assembler flags as they go by. Use that to handle 
thumb vs. arm mode differences in WriteNopData().

llvm-svn: 121219
 2010-12-08 01:16:55 +00:00
Jakob Stoklund Olesen
77e7ad803a Move RABasic::addMBBLiveIns to the base class, it is generally useful. 
Minor optimization to the use of IntervalMap iterators. They are fairly
heavyweight, so prefer SI.valid() over SI != end().

llvm-svn: 121217
 2010-12-08 01:06:06 +00:00
Owen Anderson
d00dc39a11 Simplify the byte reordering logic slightly. 
llvm-svn: 121216
 2010-12-08 00:21:33 +00:00
Owen Anderson
ba5edcfe05 VLDR fixups need special handling under Thumb. While the encoding is the same, 
the order of the bytes in the data stream is flipped around.

llvm-svn: 121215
 2010-12-08 00:18:36 +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
Devang Patel
0c0accf6bc Global variable does not need linkage name. 
llvm-svn: 121212
 2010-12-08 00:06:22 +00:00
Devang Patel
bdbff5f106 Add support to create local variable's debug info. 
llvm-svn: 121211
 2010-12-07 23:58:00 +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
Rafael Espindola
790fe1d064 Layout each section independently. With the testcase in PR8711: 
before:
        4 assembler - Number of assembler layout and relaxation steps
    78563 assembler - Number of emitted assembler fragments
  8693904 assembler - Number of emitted object file bytes
   271223 assembler - Number of evaluated fixups
330771677 assembler - Number of fragment layouts
     5958 assembler - Number of relaxed instructions
  2508361 mcexpr    - Number of MCExpr evaluations

real	0m26.123s
user	0m25.694s
sys	0m0.388s

after:

      4 assembler - Number of assembler layout and relaxation steps
  78563 assembler - Number of emitted assembler fragments
8693904 assembler - Number of emitted object file bytes
 271223 assembler - Number of evaluated fixups
 231507 assembler - Number of fragment layouts
   5958 assembler - Number of relaxed instructions
2508361 mcexpr    - Number of MCExpr evaluations

real	0m2.500s
user	0m2.113s
sys	0m0.273s

And yes, the outputs are identical :-)

llvm-svn: 121207
 2010-12-07 23:32:26 +00:00
Matt Beaumont-Gay
5e680ad101 Fix a warning about a variable which is only used in an assertion. 
llvm-svn: 121206
 2010-12-07 23:26:21 +00:00
Devang Patel
cef2982b39 Add support to create variables, structs etc.. using DIBuilder. 
This is still work in progress.

llvm-svn: 121205
 2010-12-07 23:25:47 +00:00
Jakob Stoklund Olesen
9d6472e894 Switch LiveIntervalUnion from std::set to IntervalMap. 
This speeds up RegAllocBasic by 20%, not counting releaseMemory which becomes
way faster.

llvm-svn: 121201
 2010-12-07 23:18:47 +00:00
Jakob Stoklund Olesen
87009679c3 Fix begin() and end() on const IntervalMap. 
llvm-svn: 121200
 2010-12-07 23:18:43 +00:00
Bill Wendling
45bdb13970 Cleanup in the Darwin end. No functionality change. 
llvm-svn: 121198
 2010-12-07 23:11:00 +00:00
Evan Cheng
3bd9b95b4d Fix a bad prologue / epilogue codegen bug where the compiler would emit illegal 
vpush instructions to save / restore VFP / NEON registers like this:
vpush {d8,d10,d11}
vpop {d8,d10,d11}

vpush and vpop do not allow gaps in the register list.
rdar://8728956

llvm-svn: 121197
 2010-12-07 23:08:38 +00:00
Jim Grosbach
f3557afc0f Add source Record* reference to PatternToMatch. Allows better diagnostics. 
llvm-svn: 121196
 2010-12-07 23:05:49 +00:00
Bill Wendling
4399d09458 A bit of cleanup: early exit ApplyFixup and cache the Fixup offset. No 
functionality change.

llvm-svn: 121195
 2010-12-07 23:05:20 +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