[Bug target/54051] New: Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[Bug target/54051] New: Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[ramana at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

             Bug #: 54051
           Summary: Invalid alignment specifier generated for vld3_lane_*
                    and vld3_dup_* intrinsics.
    Classification: Unclassified
           Product: gcc
           Version: 4.7.1
            Status: UNCONFIRMED
          Severity: normal
          Priority: P3
         Component: target
        AssignedTo: ramana@gcc.gnu.org
        ReportedBy: ramana@gcc.gnu.org
            Target: arm-*-*eabi
             Build: x86*


#include <arm_neon.h>

int32_t a __attribute__ ((aligned (64)));

int32x2x3_t test (void)
{
  return vld3_dup_s32 (&a);
}

int32x2x3_t test1 (void)
{
  int32x2x3_t res ;
  return vld3_lane_s32 (&a, res, 1);
}

/tmp/ccdQ3KCr.s: Assembler messages:
/tmp/ccdQ3KCr.s:24: Error: can't use alignment with this instruction --
`vld3.32 {d16[],d17[],d18[]},[r3:64]'
/tmp/ccdQ3KCr.s:50: Error: can't use alignment with this instruction --
`vld3.32 {d16[1],d17[1],d18[1]},[r3:64]'

This can be traced to the use of the Alignment specifiers in the appropriate
patterns and that needs to be fixed up.

[Bug target/54051] [4.7/ 4.8 regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[ramana at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Ramana Radhakrishnan <ramana at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Status|UNCONFIRMED                 |ASSIGNED
   Last reconfirmed|                            |2012-07-20
      Known to work|                            |4.6.3
            Summary|Invalid alignment specifier |[4.7/ 4.8 regression]
                   |generated for vld3_lane_*   |Invalid alignment specifier
                   |and vld3_dup_* intrinsics.  |generated for vld3_lane_*
                   |                            |and vld3_dup_* intrinsics.
     Ever Confirmed|0                           |1
      Known to fail|                            |4.7.0, 4.7.1

--- Comment #1 from Ramana Radhakrishnan <ramana at gcc dot gnu.org> 2012-07-20 14:35:25 UTC ---
I have a patch for this.

[Bug target/54051] [4.7/ 4.8 regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[ramana at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

--- Comment #2 from Ramana Radhakrishnan <ramana at gcc dot gnu.org> 2012-07-24 12:02:37 UTC ---
Author: ramana
Date: Tue Jul 24 12:02:30 2012
New Revision: 189808

URL: http://gcc.gnu.org/viewcvs?root=gcc&view=rev&rev=189808
Log:

Fix PR target/54051


2012-07-24  Ramana Radhakrishnan  <ramana.radhakrishnan@linaro.org>

    PR target/54051
    * config/arm/arm.c (arm_print_operand_address): Remove superfluous
    printing of 0.
    * config/arm/neon.md ("neon_vld3_lane<mode>":VD): Remove alignment
    specifier.
    ("neon_vld3_lane<mode>":VMQ): Likewise.
    ("neon_vld3_dup<mode>":VDX): Likewise.
    ("neon_vst3_lane<mode>":VD): Likewise.
    ("neon_vst3_lane<mode>":VMQ): Likewise.


2012-07-24  Ramana Radhakrishnan  <ramana.radhakrishnan@linaro.org>

    PR target/54051
    * gcc.target/arm/pr54051.c: New.
    * gcc.target/arm/vfp-1.c: Adjust test.



Added:
    trunk/gcc/testsuite/gcc.target/arm/pr54051.c
Modified:
    trunk/gcc/ChangeLog
    trunk/gcc/config/arm/arm.c
    trunk/gcc/config/arm/neon.md
    trunk/gcc/testsuite/ChangeLog
    trunk/gcc/testsuite/gcc.target/arm/vfp-1.c

[Bug target/54051] [4.7/ 4.8 regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[ramana at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Ramana Radhakrishnan <ramana at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
   Target Milestone|---                         |4.7.2

--- Comment #3 from Ramana Radhakrishnan <ramana at gcc dot gnu.org> 2012-07-24 12:47:52 UTC ---
Fixed on trunk.

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[rguenth at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Richard Guenther <rguenth at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
           Priority|P3                          |P2
            Summary|[4.7/ 4.8 regression]       |[4.7 Regression] Invalid
                   |Invalid alignment specifier |alignment specifier
                   |generated for vld3_lane_*   |generated for vld3_lane_*
                   |and vld3_dup_* intrinsics.  |and vld3_dup_* intrinsics.

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[jakub at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Jakub Jelinek <jakub at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
   Target Milestone|4.7.2                       |4.7.3

--- Comment #4 from Jakub Jelinek <jakub at gcc dot gnu.org> 2012-09-20 10:19:08 UTC ---
GCC 4.7.2 has been released.

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[joey.ye at arm dot com]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Joey Ye <joey.ye at arm dot com> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
                 CC|                            |joey.ye at arm dot com

--- Comment #5 from Joey Ye <joey.ye at arm dot com> 2013-02-05 07:45:28 UTC ---
This issue also impacts ldrexh/ldrexb as assembler doesn't accept ldrexh r1,
[r0, #0]. Better to backport to 4.7.

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[joey.ye at arm dot com]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

--- Comment #6 from Joey Ye <joey.ye at arm dot com> 2013-02-05 07:48:48 UTC ---
(In reply to comment #5)
> This issue also impacts ldrexh/ldrexb as assembler doesn't accept ldrexh r1,
> [r0, #0]. Better to backport to 4.7.

and 4.6

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[rguenth at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Richard Biener <rguenth at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
   Target Milestone|4.7.3                       |4.7.4

--- Comment #7 from Richard Biener <rguenth at gcc dot gnu.org> 2013-04-11 07:59:24 UTC ---
GCC 4.7.3 is being released, adjusting target milestone.

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[ramana at gcc dot gnu.org]

http://gcc.gnu.org/bugzilla/show_bug.cgi?id=54051

Ramana Radhakrishnan <ramana at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Status|ASSIGNED                    |NEW

--- Comment #8 from Ramana Radhakrishnan <ramana at gcc dot gnu.org> ---
Not working on this.

[Bug target/54051] [4.7 Regression] Invalid alignment specifier generated for vld3_lane_* and vld3_dup_* intrinsics.

[rguenth at gcc dot gnu.org]

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

Richard Biener <rguenth at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Status|NEW                         |RESOLVED
      Known to work|                            |4.8.0
         Resolution|---                         |FIXED
   Target Milestone|4.7.4                       |4.8.0
      Known to fail|                            |4.7.4

--- Comment #9 from Richard Biener <rguenth at gcc dot gnu.org> ---
Fixed for 4.8.0.