[Bug target/63870] New: [Aarch64] [ARM] Errors in use of NEON instrinsics are reported incorrectly

[Bug target/63870] New: [Aarch64] [ARM] Errors in use of NEON instrinsics are reported incorrectly

[cbaylis at gcc dot gnu.org]

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

            Bug ID: 63870
           Summary: [Aarch64] [ARM] Errors in use of NEON instrinsics are
                    reported incorrectly
           Product: gcc
           Version: 4.7.0
            Status: UNCONFIRMED
          Severity: normal
          Priority: P3
         Component: target
          Assignee: cbaylis at gcc dot gnu.org
          Reporter: cbaylis at gcc dot gnu.org
                CC: alan.lawrence at arm dot com
            Target: arm-unknown-linux-gnueabi, aarch64-linux-gnu

Created attachment 33972
  --> https://gcc.gnu.org/bugzilla/attachment.cgi?id=33972&action=edit
Example tests

Several NEON intrinsics have arguments which must be a constant integer in a
fixed range. At present, these constraints are enforced for most intrinsics
during assembly output, or, in some cases, not checked at all.

This can be fixed by using the %K format specifier to the error message. See 
https://gcc.gnu.org/ml/gcc-patches/2014-11/msg01248.html for a proposed patch
and explanation.

Once that patch is applied, it is necessary to rework the expansion of the
builtins so that the constraints are checked during expansion. Some of this
work has been started for Aarch64
(https://gcc.gnu.org/ml/gcc-patches/2014-11/msg00421.html)


Example demonstration of incorrect error messages using attached test cases on
an ARM target. Note that the error message is reported at the end of each
function, rather than the line where the error occurs.

$ arm-unknown-linux-gnueabihf-gcc -c neon_const_range_tests/* -mfpu=neon
neon_const_range_tests/vld1.c: In function ‘f_vld1_lane’:
neon_const_range_tests/vld1.c:10:1: error: lane out of range
 }
 ^
neon_const_range_tests/vld4.c: In function ‘f_vld4_lane’:
neon_const_range_tests/vld4.c:10:1: error: lane out of range
 }
 ^
neon_const_range_tests/vmul_lane.c: In function ‘f_vmul_lane’:
neon_const_range_tests/vmul_lane.c:10:1: error: lane out of range
 }
 ^
neon_const_range_tests/vshl.c: In function ‘f_vshl’:
neon_const_range_tests/vshl.c:10:1: error: constant out of range
 }
 ^
neon_const_range_tests/vshrn_n.c: In function ‘f_vshrn_n’:
neon_const_range_tests/vshrn_n.c:10:1: error: constant out of range
 }
 ^
neon_const_range_tests/vst1.c: In function ‘f_vst1_lane’:
neon_const_range_tests/vst1.c:9:1: error: lane out of range
 }
 ^
neon_const_range_tests/vst4.c: In function ‘f_vst4_lane’:
neon_const_range_tests/vst4.c:9:1: error: lane out of range
 }
 ^
>From gcc-bugs-return-466765-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org Fri Nov 14 13:56:36 2014
Return-Path: <gcc-bugs-return-466765-listarch-gcc-bugs=gcc.gnu.org@gcc.gnu.org>
Delivered-To: listarch-gcc-bugs@gcc.gnu.org
Received: (qmail 8282 invoked by alias); 14 Nov 2014 13:56:36 -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
Delivered-To: mailing list gcc-bugs@gcc.gnu.org
Received: (qmail 8242 invoked by uid 48); 14 Nov 2014 13:56:32 -0000
From: "redi at gcc dot gnu.org" <gcc-bugzilla@gcc.gnu.org>
To: gcc-bugs@gcc.gnu.org
Subject: [Bug go/63816] internal compiler error: in expand_expr_addr_expr_1 on gcc version 5.0.0 20141109 (experimental)
Date: Fri, 14 Nov 2014 13:56:00 -0000
X-Bugzilla-Reason: CC
X-Bugzilla-Type: changed
X-Bugzilla-Watch-Reason: None
X-Bugzilla-Product: gcc
X-Bugzilla-Component: go
X-Bugzilla-Version: unknown
X-Bugzilla-Keywords:
X-Bugzilla-Severity: normal
X-Bugzilla-Who: redi at gcc dot gnu.org
X-Bugzilla-Status: NEW
X-Bugzilla-Priority: P3
X-Bugzilla-Assigned-To: ian at airs dot com
X-Bugzilla-Target-Milestone: ---
X-Bugzilla-Flags:
X-Bugzilla-Changed-Fields: bug_status cf_reconfirmed_on everconfirmed
Message-ID: <bug-63816-4-2ipOKC7fr5@http.gcc.gnu.org/bugzilla/>
In-Reply-To: <bug-63816-4@http.gcc.gnu.org/bugzilla/>
References: <bug-63816-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: 2014-11/txt/msg01237.txt.bz2
Content-length: 527

https://gcc.gnu.org/bugzilla/show_bug.cgi?idc816

Jonathan Wakely <redi at gcc dot gnu.org> changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
             Status|UNCONFIRMED                 |NEW
   Last reconfirmed|                            |2014-11-14
     Ever confirmed|0                           |1

--- Comment #1 from Jonathan Wakely <redi at gcc dot gnu.org> ---
I'm seeing the same ICE on ppc64 with a modified libstdc++

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[alan.lawrence at arm dot com]

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

--- Comment #1 from Alan Lawrence <alan.lawrence at arm dot com> ---
Same problem on AArch64, although the error messages are a little different
(and varied) - this is following r217440 which provides some improvement in
some cases:

$ /work/alalaw01/sbuild/install/bin/aarch64-none-elf-gcc -c -O2
neon_const_range_tests/*       
In file included from neon_const_range_tests/vld1.c:2:0:
/work/alalaw01/sbuild/install/lib/gcc/aarch64-none-elf/5.0.0/include/arm_neon.h:
In function 'f_vld1_lane':
/work/alalaw01/sbuild/install/lib/gcc/aarch64-none-elf/5.0.0/include/arm_neon.h:658:10:
error: lane -1 out of range 0 - 7
   return __aarch64_vset_lane_any (__vec, __index, __elem, 8);
          ^
In file included from neon_const_range_tests/vld4.c:2:0:
/work/alalaw01/sbuild/install/lib/gcc/aarch64-none-elf/5.0.0/include/arm_neon.h:
In function 'f_vld4_lane':
/work/alalaw01/sbuild/install/lib/gcc/aarch64-none-elf/5.0.0/include/arm_neon.h:18111:1:
error: lane -1 out of range 0 - 15
 __LD4_LANE_FUNC (int8x8x4_t, int8x8_t, int8x16x4_t, int8_t, v16qi, qi, s8,
 ^
/tmp/ccKedD22.s: Assembler messages:
/tmp/ccKedD22.s:9: Error: register element index out of range 0 to 7 at operand
3 -- `mul v0.8h,v0.8h,v1.h[-1]'
/tmp/ccKedD22.s: Assembler messages:
/tmp/ccKedD22.s:10: Error: immediate value out of range 1 to 8 at operand 3 --
`shrn v0.8b,v0.8h,9'

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[cbaylis at gcc dot gnu.org]

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

--- Comment #2 from cbaylis at gcc dot gnu.org ---
Author: cbaylis
Date: Thu Nov 20 16:26:54 2014
New Revision: 217885

URL: https://gcc.gnu.org/viewcvs?rev=217885&root=gcc&view=rev
Log:
        PR target/63870
        * config/aarch64/aarch64-builtins.c (aarch64_simd_expand_args): Pass
        expression to aarch64_simd_lane_bounds.
        * config/aarch64/aarch64-protos.h (aarch64_simd_lane_bounds): Update
        prototype.
        * config/aarch64/aarch64-simd.md: (aarch64_combinez<mode>): Update
        call to aarch64_simd_lane_bounds.
        (aarch64_get_lanedi): Likewise.
        (aarch64_ld2_lane<mode>): Likewise.
        (aarch64_ld3_lane<mode>): Likewise.
        (aarch64_ld4_lane<mode>): Likewise.
        (aarch64_im_lane_boundsi): Likewise.
        * config/aarch64/aarch64.c (aarch64_simd_lane_bounds): Add exp
        parameter. Report calling function in error message if exp is non-NULL.


Modified:
    trunk/gcc/ChangeLog
    trunk/gcc/config/aarch64/aarch64-builtins.c
    trunk/gcc/config/aarch64/aarch64-protos.h
    trunk/gcc/config/aarch64/aarch64-simd.md
    trunk/gcc/config/aarch64/aarch64.c

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[ramana at gcc dot gnu.org]

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

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

           What    |Removed                     |Added
----------------------------------------------------------------------------
           Keywords|                            |diagnostic
             Status|UNCONFIRMED                 |NEW
   Last reconfirmed|                            |2014-11-27
     Ever confirmed|0                           |1

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[alalaw01 at gcc dot gnu.org]

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

--- Comment #3 from alalaw01 at gcc dot gnu.org ---
Author: alalaw01
Date: Tue Dec  9 20:23:36 2014
New Revision: 218536

URL: https://gcc.gnu.org/viewcvs?rev=218536&root=gcc&view=rev
Log:
[AArch64]Remove be_checked_get_lane, check bounds with
__builtin_aarch64_im_lane_boundsi.

gcc/:

    PR target/63870
    * config/aarch64/aarch64-simd-builtins.def (be_checked_get_lane):
    Delete.
    * config/aarch64/aarch64-simd.md (aarch64_be_checked_get_lane<mode\>):
    Delete.
    * config/aarch64/arm_neon.h (aarch64_vget_lane_any): Use GCC
    vector extensions, __aarch64_lane, __builtin_aarch64_im_lane_boundsi.
    (__aarch64_vget_lane_f32, __aarch64_vget_lane_f64,
    __aarch64_vget_lane_p8, __aarch64_vget_lane_p16,
    __aarch64_vget_lane_s8, __aarch64_vget_lane_s16,
    __aarch64_vget_lane_s32, __aarch64_vget_lane_s64,
    __aarch64_vget_lane_u8, __aarch64_vget_lane_u16,
    __aarch64_vget_lane_u32, __aarch64_vget_lane_u64,
    __aarch64_vgetq_lane_f32, __aarch64_vgetq_lane_f64,
    __aarch64_vgetq_lane_p8, __aarch64_vgetq_lane_p16,
    __aarch64_vgetq_lane_s8, __aarch64_vgetq_lane_s16,
    __aarch64_vgetq_lane_s32, __aarch64_vgetq_lane_s64,
    __aarch64_vgetq_lane_u8, __aarch64_vgetq_lane_u16,
    __aarch64_vgetq_lane_u32, __aarch64_vgetq_lane_u64): Delete.
    (__aarch64_vdup_lane_any): Use __aarch64_vget_lane_any, remove
    'q2' argument.
    (__aarch64_vdup_lane_f32, __aarch64_vdup_lane_f64,
    __aarch64_vdup_lane_p8, __aarch64_vdup_lane_p16,
    __aarch64_vdup_lane_s8, __aarch64_vdup_lane_s16,
    __aarch64_vdup_lane_s32, __aarch64_vdup_lane_s64,
    __aarch64_vdup_lane_u8, __aarch64_vdup_lane_u16,
    __aarch64_vdup_lane_u32, __aarch64_vdup_lane_u64,
    __aarch64_vdup_laneq_f32, __aarch64_vdup_laneq_f64,
    __aarch64_vdup_laneq_p8, __aarch64_vdup_laneq_p16,
    __aarch64_vdup_laneq_s8, __aarch64_vdup_laneq_s16,
    __aarch64_vdup_laneq_s32, __aarch64_vdup_laneq_s64,
    __aarch64_vdup_laneq_u8, __aarch64_vdup_laneq_u16,
    __aarch64_vdup_laneq_u32, __aarch64_vdup_laneq_u64): Remove argument
    to __aarch64_vdup_lane_any.
    (vget_lane_f32, vget_lane_f64, vget_lane_p8, vget_lane_p16,
    vget_lane_s8, vget_lane_s16, vget_lane_s32, vget_lane_s64,
    vget_lane_u8, vget_lane_u16, vget_lane_u32, vget_lane_u64,
    vgetq_lane_f32, vgetq_lane_f64, vgetq_lane_p8, vgetq_lane_p16,
    vgetq_lane_s8, vgetq_lane_s16, vgetq_lane_s32, vgetq_lane_s64,
    vgetq_lane_u8, vgetq_lane_u16, vgetq_lane_u32, vgetq_lane_u64,
    vdupb_lane_p8, vdupb_lane_s8, vdupb_lane_u8, vduph_lane_p16,
    vduph_lane_s16, vduph_lane_u16, vdups_lane_f32, vdups_lane_s32,
    vdups_lane_u32, vdupb_laneq_p8, vdupb_laneq_s8, vdupb_laneq_u8,
    vduph_laneq_p16, vduph_laneq_s16, vduph_laneq_u16, vdups_laneq_f32,
    vdups_laneq_s32, vdups_laneq_u32, vdupd_laneq_f64, vdupd_laneq_s64,
    vdupd_laneq_u64, vfmas_lane_f32, vfma_laneq_f64, vfmad_laneq_f64,
    vfmas_laneq_f32, vfmss_lane_f32, vfms_laneq_f64, vfmsd_laneq_f64,
    vfmss_laneq_f32, vmla_lane_f32, vmla_lane_s16, vmla_lane_s32,
    vmla_lane_u16, vmla_lane_u32, vmla_laneq_f32, vmla_laneq_s16,
    vmla_laneq_s32, vmla_laneq_u16, vmla_laneq_u32, vmlaq_lane_f32,
    vmlaq_lane_s16, vmlaq_lane_s32, vmlaq_lane_u16, vmlaq_lane_u32,
    vmlaq_laneq_f32, vmlaq_laneq_s16, vmlaq_laneq_s32, vmlaq_laneq_u16,
    vmlaq_laneq_u32, vmls_lane_f32, vmls_lane_s16, vmls_lane_s32,
    vmls_lane_u16, vmls_lane_u32, vmls_laneq_f32, vmls_laneq_s16,
    vmls_laneq_s32, vmls_laneq_u16, vmls_laneq_u32, vmlsq_lane_f32,
    vmlsq_lane_s16, vmlsq_lane_s32, vmlsq_lane_u16, vmlsq_lane_u32,
    vmlsq_laneq_f32, vmlsq_laneq_s16, vmlsq_laneq_s32, vmlsq_laneq_u16,
    vmlsq_laneq_u32, vmul_lane_f32, vmul_lane_s16, vmul_lane_s32,
    vmul_lane_u16, vmul_lane_u32, vmuld_lane_f64, vmuld_laneq_f64,
    vmuls_lane_f32, vmuls_laneq_f32, vmul_laneq_f32, vmul_laneq_f64,
    vmul_laneq_s16, vmul_laneq_s32, vmul_laneq_u16, vmul_laneq_u32,
    vmulq_lane_f32, vmulq_lane_s16, vmulq_lane_s32, vmulq_lane_u16,
    vmulq_lane_u32, vmulq_laneq_f32, vmulq_laneq_f64, vmulq_laneq_s16,
    vmulq_laneq_s32, vmulq_laneq_u16, vmulq_laneq_u32) : Use
    __aarch64_vget_lane_any.

gcc/testsuite/:

    * gcc.target/aarch64/simd/vget_lane_f32_indices_1.c: New test.
    * gcc.target/aarch64/simd/vget_lane_f64_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_p16_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_p8_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_s16_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_s32_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_s64_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_s8_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_u16_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_u32_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_u64_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vget_lane_u8_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_f32_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_f64_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_p16_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_p8_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_s16_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_s32_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_s64_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_s8_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_u16_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_u32_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_u64_indices_1.c: Likewise.
    * gcc.target/aarch64/simd/vgetq_lane_u8_indices_1.c: Likewise.


Added:
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_f32_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_f64_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_p16_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_p8_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_s16_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_s32_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_s64_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_s8_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_u16_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_u32_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_u64_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vget_lane_u8_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_f32_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_f64_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_p16_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_p8_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_s16_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_s32_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_s64_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_s8_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_u16_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_u32_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_u64_indices_1.c
    trunk/gcc/testsuite/gcc.target/aarch64/simd/vgetq_lane_u8_indices_1.c
Modified:
    trunk/gcc/ChangeLog
    trunk/gcc/config/aarch64/aarch64-simd-builtins.def
    trunk/gcc/config/aarch64/aarch64-simd.md
    trunk/gcc/config/aarch64/arm_neon.h
    trunk/gcc/testsuite/ChangeLog

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[alalaw01 at gcc dot gnu.org]

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

alalaw01 at gcc dot gnu.org changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
                 CC|                            |alalaw01 at gcc dot gnu.org

--- Comment #4 from alalaw01 at gcc dot gnu.org ---
(Apologies for out-of-orderness, I missed PRs from logs so adding by hand)

Author: alalaw01
Date: Tue Dec  9 19:52:22 2014
Revision: 218532

https://gcc.gnu.org/viewcvs?rev=218532&root=gcc&view=rev
Log:
[AArch64] Fix ICE on non-constant indices to __builtin_aarch64_im_lane_boundsi

gcc/:

        * config/aarch64/aarch64-builtins.c (aarch64_types_binopv_qualifiers,
        TYPES_BINOPV): Delete.
        (enum aarch64_builtins): Add AARCH64_BUILTIN_SIMD_LANE_CHECK and
        AARCH64_SIMD_PATTERN_START.
        (aarch64_init_simd_builtins): Register
        __builtin_aarch64_im_lane_boundsi; use  AARCH64_SIMD_PATTERN_START.
        (aarch64_simd_expand_builtin): Handle AARCH64_BUILTIN_LANE_CHECK; use
        AARCH64_SIMD_PATTERN_START.

        * config/aarch64/aarch64-simd.md (aarch64_im_lane_boundsi): Delete.
        * config/aarch64/aarch64-simd-builtins.def (im_lane_bound): Delete.

        * config/aarch64/arm_neon.h (__AARCH64_LANE_CHECK): New.
        (__aarch64_vget_lane_f64, __aarch64_vget_lane_s64,
        __aarch64_vget_lane_u64, __aarch64_vset_lane_any, vdupd_lane_f64,
        vdupd_lane_s64, vdupd_lane_u64, vext_f32, vext_f64, vext_p8, vext_p16,
        vext_s8, vext_s16, vext_s32, vext_s64, vext_u8, vext_u16, vext_u32,
        vext_u64, vextq_f32, vextq_f64, vextq_p8, vextq_p16, vextq_s8,
        vextq_s16, vextq_s32, vextq_s64, vextq_u8, vextq_u16, vextq_u32,
        vextq_u64, vmulq_lane_f64): Use __AARCH64_LANE_CHECK.

gcc/testsuite/:

        * gcc.target/aarch64/simd/vset_lane_s16_const_1.c: New test.

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[ktkachov at gcc dot gnu.org]

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

ktkachov at gcc dot gnu.org changed:

           What    |Removed                     |Added
----------------------------------------------------------------------------
                 CC|                            |ktkachov at gcc dot gnu.org

--- Comment #5 from ktkachov at gcc dot gnu.org ---
Can this be closed now?

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[cbaylis at gcc dot gnu.org]

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

--- Comment #6 from cbaylis at gcc dot gnu.org ---
There is still a lot to do. I have patches in progress for Aarch64 loads and
stores. Aarch64 shifts still need doing, and everything for ARM.

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[alalaw01 at gcc dot gnu.org]

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

--- Comment #7 from alalaw01 at gcc dot gnu.org ---
I'm doing some of the ARM work atm, but not sure how far I'll get before stage
4 starts.

[Bug target/63870] [Aarch64] [ARM] Errors in use of NEON intrinsics are reported incorrectly

[alalaw01 at gcc dot gnu.org]

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

--- Comment #10 from alalaw01 at gcc dot gnu.org ---
Author: alalaw01
Date: Tue Sep  8 19:43:39 2015
New Revision: 227557

URL: https://gcc.gnu.org/viewcvs?rev=227557&root=gcc&view=rev
Log:
ARM/AArch64 Testsuite] Add float16 lane_f16_indices tests

        PR target/63870
        * gcc.target/aarch64/advsimd-intrinsics/vld2_lane_f16_indices_1.c: New.
        * gcc.target/aarch64/advsimd-intrinsics/vld2q_lane_f16_indices_1.c:
New.
        * gcc.target/aarch64/advsimd-intrinsics/vld3_lane_f16_indices_1.c: New.
        * gcc.target/aarch64/advsimd-intrinsics/vld3q_lane_f16_indices_1.c:
New.
        * gcc.target/aarch64/advsimd-intrinsics/vld4_lane_f16_indices_1.c: New.
        * gcc.target/aarch64/advsimd-intrinsics/vld4q_lane_f16_indices_1.c:
New.
        * gcc.target/aarch64/advsimd-intrinsics/vst2_lane_f16_indices_1.c: New.
        * gcc.target/aarch64/advsimd-intrinsics/vst2q_lane_f16_indices_1.c:
New.
        * gcc.target/aarch64/advsimd-intrinsics/vst3_lane_f16_indices_1.c: New.
        * gcc.target/aarch64/advsimd-intrinsics/vst3q_lane_f16_indices_1.c:
New.
        * gcc.target/aarch64/advsimd-intrinsics/vst4_lane_f16_indices_1.c: New.
        * gcc.target/aarch64/advsimd-intrinsics/vst4q_lane_f16_indices_1.c:
New.

Added:
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vld2_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vld2q_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vld3_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vld3q_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vld4_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vld4q_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vst2_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vst2q_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vst3_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vst3q_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vst4_lane_f16_indices_1.c
   
trunk/gcc/testsuite/gcc.target/aarch64/advsimd-intrinsics/vst4q_lane_f16_indices_1.c
Modified:
    trunk/gcc/testsuite/ChangeLog