aboutsummaryrefslogtreecommitdiff
diff options
context:
space:
mode:
authorAlan Modra <amodra@gmail.com>2016-08-10 15:13:36 +0930
committerAlan Modra <amodra@gcc.gnu.org>2016-08-10 15:13:36 +0930
commitc4e9cff61cfdad1a86927019df6bf27abef2709f (patch)
treec59c5d35f65562c7e1b8347eaa3db0fad9510d1f
parent6bbd98101c27fc011dd778be8b0ec805dccf0e56 (diff)
downloadgcc-c4e9cff61cfdad1a86927019df6bf27abef2709f.zip
gcc-c4e9cff61cfdad1a86927019df6bf27abef2709f.tar.gz
gcc-c4e9cff61cfdad1a86927019df6bf27abef2709f.tar.bz2
[RS6000] e500 part of pr71680
The fallback part of HARD_REGNO_CALLER_SAVE_MODE, choose_hard_reg_mode, returns DFmode for SImode when TARGET_E500_DOUBLE. This confuses lra when attempting to save ctr around a call. PR target/71680 * config/rs6000/rs6000.h (HARD_REGNO_CALLER_SAVE_MODE): Return SImode for TARGET_E500_DOUBLE when given SImode. From-SVN: r239317
-rw-r--r--gcc/ChangeLog6
-rw-r--r--gcc/config/rs6000/rs6000.h2
2 files changed, 8 insertions, 0 deletions
diff --git a/gcc/ChangeLog b/gcc/ChangeLog
index dba02c5..7b8cbc7 100644
--- a/gcc/ChangeLog
+++ b/gcc/ChangeLog
@@ -1,3 +1,9 @@
+2016-08-10 Alan Modra <amodra@gmail.com>
+
+ PR target/71680
+ * config/rs6000/rs6000.h (HARD_REGNO_CALLER_SAVE_MODE): Return
+ SImode for TARGET_E500_DOUBLE when given SImode.
+
2016-08-09 David Wohlferd <dw@LimeGreenSocks.com>
* config/i3836/avx512fintrin.h (_mm512_cvtsepi64_epi32): Remove
diff --git a/gcc/config/rs6000/rs6000.h b/gcc/config/rs6000/rs6000.h
index af77258..353f388 100644
--- a/gcc/config/rs6000/rs6000.h
+++ b/gcc/config/rs6000/rs6000.h
@@ -1273,6 +1273,8 @@ enum data_align { align_abi, align_opt, align_both };
&& ((MODE) == VOIDmode || ALTIVEC_OR_VSX_VECTOR_MODE (MODE)) \
&& FP_REGNO_P (REGNO) \
? V2DFmode \
+ : TARGET_E500_DOUBLE && (MODE) == SImode \
+ ? SImode \
: TARGET_E500_DOUBLE && ((MODE) == VOIDmode || (MODE) == DFmode) \
? DFmode \
: !TARGET_E500_DOUBLE && FLOAT128_IBM_P (MODE) && FP_REGNO_P (REGNO) \