summaryrefslogtreecommitdiff
diff options
context:
space:
mode:
authoramodra <amodra@138bc75d-0d04-0410-961f-82ee72b054a4>2016-08-10 05:43:36 +0000
committeramodra <amodra@138bc75d-0d04-0410-961f-82ee72b054a4>2016-08-10 05:43:36 +0000
commit081a6ff0f79d63a83a561d8178baabcad5c7ff08 (patch)
treec59c5d35f65562c7e1b8347eaa3db0fad9510d1f
parent364d61e55dc466f8470789cfeac7f54b905a3d65 (diff)
downloadgcc-081a6ff0f79d63a83a561d8178baabcad5c7ff08.tar.gz
[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. git-svn-id: svn+ssh://gcc.gnu.org/svn/gcc/trunk@239317 138bc75d-0d04-0410-961f-82ee72b054a4
-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 dba02c53cae..7b8cbc7ad2f 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 af77258f1e3..353f388d770 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) \