[PATCH] [PowerPC] Fix __tls_get_addr sequence to avoid register assignment issues

[hfinkel at anl.gov]

In http://reviews.llvm.org/D7491#120413, @wschmidt wrote:

> Re-posting the last one because PPCTLSDynamicCall.cpp came out as a diff instead of an add of a new file.  Sorry for any problems.


Unfortunately, I see the same problem here that caused me to revert the previous version. Even leaving Clang untouched (so we still get the linker flag to disable the tls optimizations), self-hosting fails on the `P7`:

  Building arm_neon.h...
  0  clang-tblgen 0x000000001009fdb4
  1  clang-tblgen 0x00000000100a0cb4
  2  clang-tblgen 0x00000000100a0f64
  3               0x00000fff8a020448 __kernel_sigtramp_rt64 + 0
  4  clang-tblgen 0x000000001008d29c
  5  clang-tblgen 0x000000001007d6ec
  6  libc.so.6    0x00000080b782c088
  7  libc.so.6    0x00000080b782c280 __libc_start_main + 4293375408
  /bin/sh: line 1: 36646 Segmentation fault      (core dumped) ../../../../bin/clang-tblgen -gen-arm-neon -I/home/hfinkel/src/llvm/tools/clang/lib/Headers -I /home/hfinkel/src/llvm/lib/Target -I /home/hfinkel/src/llvm/include /home/hfinkel/src/llvm/tools/clang/include/clang/Basic/arm_neon.td -o /home/hfinkel/build/ppc64/llvm-stage1/tools/clang/lib/Headers/arm_neon.h.tmp
  make[2]: *** [tools/clang/lib/Headers/arm_neon.h.tmp] Error 139

This is a cmake self-hosted build, gcc 4.8.2 providing the libstdc++, -O3 -mcpu=native -DNDEBUG.


http://reviews.llvm.org/D7491

EMAIL PREFERENCES
  http://reviews.llvm.org/settings/panel/emailpreferences/