From patchwork Thu Nov 4 02:45:41 2010 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: "H.J. Lu" X-Patchwork-Id: 70095 Return-Path: X-Original-To: incoming@patchwork.ozlabs.org Delivered-To: patchwork-incoming@bilbo.ozlabs.org Received: from sourceware.org (server1.sourceware.org [209.132.180.131]) by ozlabs.org (Postfix) with SMTP id C705EB70A7 for ; Thu, 4 Nov 2010 13:46:06 +1100 (EST) Received: (qmail 27439 invoked by alias); 4 Nov 2010 02:46:04 -0000 Received: (qmail 27425 invoked by uid 22791); 4 Nov 2010 02:46:03 -0000 X-SWARE-Spam-Status: No, hits=-1.3 required=5.0 tests=AWL, BAYES_00, NO_DNS_FOR_FROM, TW_AV, TW_VZ, T_RP_MATCHES_RCVD X-Spam-Check-By: sourceware.org Received: from mga03.intel.com (HELO mga03.intel.com) (143.182.124.21) by sourceware.org (qpsmtpd/0.43rc1) with ESMTP; Thu, 04 Nov 2010 02:45:59 +0000 Received: from azsmga001.ch.intel.com ([10.2.17.19]) by azsmga101.ch.intel.com with ESMTP; 03 Nov 2010 19:45:57 -0700 X-ExtLoop1: 1 Received: from gnu-6.sc.intel.com ([10.3.194.135]) by azsmga001.ch.intel.com with ESMTP; 03 Nov 2010 19:45:41 -0700 Received: by gnu-6.sc.intel.com (Postfix, from userid 500) id 913F4207F0; Wed, 3 Nov 2010 19:45:41 -0700 (PDT) Date: Wed, 3 Nov 2010 19:45:41 -0700 From: "H.J. Lu" To: gcc-patches@gcc.gnu.org, Uros Bizjak Subject: Re: PATCH: PR target/46285: ICE: in final_scan_insn, at final.c:2642 with -mavx -fsplit-stack Message-ID: <20101104024541.GA661@intel.com> Reply-To: "H.J. Lu" References: <20101103044253.GA771@intel.com> MIME-Version: 1.0 Content-Disposition: inline In-Reply-To: <20101103044253.GA771@intel.com> User-Agent: Mutt/1.5.21 (2010-09-15) Mailing-List: contact gcc-patches-help@gcc.gnu.org; run by ezmlm Precedence: bulk List-Id: List-Unsubscribe: List-Archive: List-Post: List-Help: Sender: gcc-patches-owner@gcc.gnu.org Delivered-To: mailing list gcc-patches@gcc.gnu.org On Tue, Nov 02, 2010 at 09:42:53PM -0700, H.J. Lu wrote: > Hi, > > We should generate avx_vzeroupper after reload is completed. OK for > trunk? > > Thanks. > > > H.J. > --- > gcc/ > > 2010-11-02 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-02 H.J. Lu > > PR target/46285 > * gcc.target/i386/pr46285.c. > Hi, I checked in this patch as an obvious fix. Thanks. H.J. Index: gcc.target/i386/pr46285.c =================================================================== --- gcc.target/i386/pr46285.c (revision 166297) +++ gcc.target/i386/pr46285.c (working copy) @@ -1,5 +1,6 @@ /* { dg-do compile } */ /* { dg-options "-mavx -fsplit-stack -mtune=generic" } */ +/* { dg-require-effective-target split_stack } */ typedef char __m256 __attribute__ ((__vector_size__ (32))); void foo (__m256 x) {} Index: ChangeLog =================================================================== --- ChangeLog (revision 166297) +++ ChangeLog (working copy) @@ -1,3 +1,7 @@ +2010-11-03 H.J. Lu + + * gcc.target/i386/pr46285.c: Require split_stack target. + 2010-11-03 Jason Merrill PR c++/46293