From 72fdf9e9c4c469d8ca5abf63c7ace0c6a7569f49 Mon Sep 17 00:00:00 2001 From: "H.J. Lu" Date: Wed, 3 Nov 2010 12:02:06 +0000 Subject: [PATCH] Generate avx_vzeroupper after reload is completed. gcc/ 2010-11-03 H.J. Lu PR target/46285 * config/i386/i386.c (ix86_expand_call): Conditionally decorate calls with UNSPEC_CALL_NEEDS_VZEROUPPER unspec before reload is completed. gcc/testsuite/ 2010-11-03 H.J. Lu PR target/46285 * gcc.target/i386/pr46285.c. From-SVN: r166240 --- gcc/ChangeLog | 7 +++++++ gcc/config/i386/i386.c | 14 ++++++++++---- gcc/testsuite/ChangeLog | 5 +++++ gcc/testsuite/gcc.target/i386/pr46285.c | 5 +++++ 4 files changed, 27 insertions(+), 4 deletions(-) create mode 100644 gcc/testsuite/gcc.target/i386/pr46285.c diff --git a/gcc/ChangeLog b/gcc/ChangeLog index 76ebd7e8236..55b233d3318 100644 --- a/gcc/ChangeLog +++ b/gcc/ChangeLog @@ -1,3 +1,10 @@ +2010-11-03 H.J. Lu + + PR target/46285 + * config/i386/i386.c (ix86_expand_call): Conditionally decorate + calls with UNSPEC_CALL_NEEDS_VZEROUPPER unspec before reload + is completed. + 2010-11-03 Richard Guenther PR tree-optimization/46217 diff --git a/gcc/config/i386/i386.c b/gcc/config/i386/i386.c index afecc8935da..ba1e4fc5149 100644 --- a/gcc/config/i386/i386.c +++ b/gcc/config/i386/i386.c @@ -21540,10 +21540,16 @@ ix86_expand_call (rtx retval, rtx fnaddr, rtx callarg1, else avx256 = call_no_avx256; - unspec = gen_rtx_UNSPEC (VOIDmode, - gen_rtvec (1, GEN_INT (avx256)), - UNSPEC_CALL_NEEDS_VZEROUPPER); - call = gen_rtx_PARALLEL (VOIDmode, gen_rtvec (2, call, unspec)); + if (reload_completed) + emit_insn (gen_avx_vzeroupper (GEN_INT (avx256))); + else + { + unspec = gen_rtx_UNSPEC (VOIDmode, + gen_rtvec (1, GEN_INT (avx256)), + UNSPEC_CALL_NEEDS_VZEROUPPER); + call = gen_rtx_PARALLEL (VOIDmode, + gen_rtvec (2, call, unspec)); + } } call = emit_call_insn (call); diff --git a/gcc/testsuite/ChangeLog b/gcc/testsuite/ChangeLog index 86ff763f05c..29f4dc3b819 100644 --- a/gcc/testsuite/ChangeLog +++ b/gcc/testsuite/ChangeLog @@ -1,3 +1,8 @@ +2010-11-03 H.J. Lu + + PR target/46285 + * gcc.target/i386/pr46285.c. + 2010-11-03 Richard Guenther PR tree-optimization/46217 diff --git a/gcc/testsuite/gcc.target/i386/pr46285.c b/gcc/testsuite/gcc.target/i386/pr46285.c new file mode 100644 index 00000000000..8b8cbcf0f18 --- /dev/null +++ b/gcc/testsuite/gcc.target/i386/pr46285.c @@ -0,0 +1,5 @@ +/* { dg-do compile } */ +/* { dg-options "-mavx -fsplit-stack -mtune=generic" } */ + +typedef char __m256 __attribute__ ((__vector_size__ (32))); +void foo (__m256 x) {}