From mboxrd@z Thu Jan  1 00:00:00 1970
Return-Path: <gcc-bugs-return-479903-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Received: (qmail 66612 invoked by alias); 10 Mar 2015 08:15:35 -0000
Mailing-List: contact gcc-bugs-help@gcc.gnu.org; run by ezmlm
Precedence: bulk
List-Id: <gcc-bugs.gcc.gnu.org>
List-Archive: <http://gcc.gnu.org/ml/gcc-bugs/>
List-Post: <mailto:gcc-bugs@gcc.gnu.org>
List-Help: <mailto:gcc-bugs-help@gcc.gnu.org>
Sender: gcc-bugs-owner@gcc.gnu.org
Received: (qmail 66575 invoked by uid 48); 10 Mar 2015 08:15:31 -0000
From: "kugan at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug target/65375] New: poor codegen for ld[234]/st[234]
Date: Tue, 10 Mar 2015 08:15:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: new
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: target
X-Bugzilla-Version: 5.0
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: kugan at gcc dot gnu.org
X-Bugzilla-Status: UNCONFIRMED
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: unassigned at gcc dot gnu.org
X-Bugzilla-Target-Milestone: ---
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields: bug_id short_desc product version bug_status bug_severity priority component assigned_to reporter
Message-ID: <bug-65375-4@http.gcc.gnu.org/bugzilla/>
Content-Type: text/plain; charset="UTF-8"
Content-Transfer-Encoding: 7bit
X-Bugzilla-URL: http://gcc.gnu.org/bugzilla/
Auto-Submitted: auto-generated
MIME-Version: 1.0
X-SW-Source: 2015-03/txt/msg01047.txt.bz2

https://gcc.gnu.org/bugzilla/show_bug.cgi?id=65375

            Bug ID: 65375
           Summary: poor codegen for ld[234]/st[234]
           Product: gcc
           Version: 5.0
            Status: UNCONFIRMED
          Severity: normal
          Priority: P3
         Component: target
          Assignee: unassigned at gcc dot gnu.org
          Reporter: kugan at gcc dot gnu.org

#include <arm_neon.h>
void hello_vst2(float* fout, float *fin)
{
float32x4x2_t a;
a = vld2q_f32 (fin);
vst2q_f32 (fout, a);
}


with aarch64-none-linux-gnu-gcc  -O2 -ffast-math -unsafe-math-optimisations
produces:

    .cpu generic+fp+simd
    .file    "neon.c"
    .text
    .align    2
    .p2align 3,,7
    .global    hello_vst2
    .type    hello_vst2, %function
hello_vst2:
    ld2    {v0.4s - v1.4s}, [x1]
    sub    sp, sp, #32
    umov    x1, v0.d[0]
    umov    x2, v0.d[1]
    str    q1, [sp, 16]
    mov    x5, x1
    stp    x5, x2, [sp]
    ld1    {v0.16b - v1.16b}, [sp]
    st2    {v0.4s - v1.4s}, [x0]
    add    sp, sp, 32
    ret
    .size    hello_vst2, .-hello_vst2
    .ident    "GCC: (GNU) 5.0.0 20150305 (experimental)"
    .section    .note.GNU-stack,"",%progbits