File: neon-cond-1.c

package info (click to toggle)
gcc-arm-none-eabi 15%3A8-2019-q3-1
  • links: PTS, VCS
  • area: main
  • in suites: bullseye
  • size: 571,828 kB
  • sloc: ansic: 2,937,651; cpp: 881,644; ada: 597,189; makefile: 65,528; asm: 56,499; xml: 46,621; exp: 24,747; sh: 19,684; python: 7,256; pascal: 4,370; awk: 3,497; perl: 2,695; yacc: 316; ml: 285; f90: 234; lex: 198; objc: 194; haskell: 119
file content (31 lines) | stat: -rw-r--r-- 728 bytes parent folder | download | duplicates (10) 
1
2
3
4
5
6
7
8
9
10
11
12
13
14
15
16
17
18
19
20
21
22
23
24
25
26
27
28
29
30
31
 
/* { dg-do run } */
/* { dg-require-effective-target arm_neon_hw } */
/* { dg-options "-O2" } */
/* { dg-add-options arm_neon } */
/* Check that the arm_final_prescan_insn ccfsm code does not try to
 * conditionally execute NEON instructions.  */
#include <arm_neon.h>
#include <stdlib.h>

int __attribute__((noinline))
foo(uint32x2_t a, uint32_t *p, uint32_t *q)
{
  if (p != q)
    /* This vst1 instruction could be conditional, except that NEON
       instructions are never conditional in ARM mode.  */
    vst1_u32(p, a);
  return 0;
}

int
main()
{
    uint32x2_t v;
    uint32_t a[2] = {1, 42};
    v = vld1_u32(a);
    v = vadd_u32(v, v);
    foo(v, a, a);
    if (a[0] != 1 || a[1] != 42)
      abort();
    exit(0);
}