1  /* { dg-do run } */
       2  /* { dg-require-effective-target arm_v8_2a_fp16_neon_hw } */
       3  /* { dg-add-options arm_v8_2a_fp16_neon } */
       4  /* { dg-skip-if "" { arm*-*-* } } */
       5  
       6  #include <arm_neon.h>
       7  #include "arm-neon-ref.h"
       8  #include "compute-ref-data.h"
       9  
      10  #define FP16_C(a) ((__fp16) a)
      11  #define A0 FP16_C (123.4)
      12  #define B0 FP16_C (-567.8)
      13  #define C0 FP16_C (34.8)
      14  #define D0 FP16_C (0.0)
      15  
      16  #define A1 FP16_C (1025.8)
      17  #define B1 FP16_C (13.4)
      18  #define C1 FP16_C (-567.8)
      19  #define D1 FP16_C (10)
      20  #define E1 FP16_C (-0.0)
      21  #define F1 FP16_C (567.8)
      22  #define G1 FP16_C (0.0)
      23  #define H1 FP16_C (10)
      24  
      25  /* Expected results for vmaxv.  */
      26  uint16_t expect = 0x57B6 /* A0.  */;
      27  uint16_t expect_alt = 0x6402 /* A1.  */;
      28  
      29  void exec_vmaxv_f16 (void)
      30  {
      31  #undef TEST_MSG
      32  #define TEST_MSG "VMAXV (FP16)"
      33    clean_results ();
      34  
      35    DECL_VARIABLE(vsrc, float, 16, 4);
      36    VECT_VAR_DECL (buf_src, float, 16, 4) [] = {A0, B0, C0, D0};
      37    VLOAD (vsrc, buf_src, , float, f, 16, 4);
      38    float16_t vector_res = vmaxv_f16 (VECT_VAR (vsrc, float, 16, 4));
      39  
      40    if (* (uint16_t *) &vector_res != expect)
      41      abort ();
      42  
      43    VECT_VAR_DECL (buf_src1, float, 16, 4) [] = {B0, A0, C0, D0};
      44    VLOAD (vsrc, buf_src1, , float, f, 16, 4);
      45    vector_res = vmaxv_f16 (VECT_VAR (vsrc, float, 16, 4));
      46  
      47    if (* (uint16_t *) &vector_res != expect)
      48      abort ();
      49  
      50    VECT_VAR_DECL (buf_src2, float, 16, 4) [] = {B0, C0, A0, D0};
      51    VLOAD (vsrc, buf_src2, , float, f, 16, 4);
      52    vector_res = vmaxv_f16 (VECT_VAR (vsrc, float, 16, 4));
      53  
      54    if (* (uint16_t *) &vector_res != expect)
      55      abort ();
      56  
      57    VECT_VAR_DECL (buf_src3, float, 16, 4) [] = {B0, C0, D0, A0};
      58    VLOAD (vsrc, buf_src3, , float, f, 16, 4);
      59    vector_res = vmaxv_f16 (VECT_VAR (vsrc, float, 16, 4));
      60  
      61    if (* (uint16_t *) &vector_res != expect)
      62      abort ();
      63  
      64  #undef TEST_MSG
      65  #define TEST_MSG "VMAXVQ (FP16)"
      66    clean_results ();
      67  
      68    DECL_VARIABLE(vsrc, float, 16, 8);
      69    VECT_VAR_DECL (buf_src, float, 16, 8) [] = {A1, B1, C1, D1, E1, F1, G1, H1};
      70    VLOAD (vsrc, buf_src, q, float, f, 16, 8);
      71    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
      72  
      73    if (* (uint16_t *) &vector_res != expect_alt)
      74      abort ();
      75  
      76    VECT_VAR_DECL (buf_src1, float, 16, 8) [] = {B1, A1, C1, D1, E1, F1, G1, H1};
      77    VLOAD (vsrc, buf_src1, q, float, f, 16, 8);
      78    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
      79  
      80    if (* (uint16_t *) &vector_res != expect_alt)
      81      abort ();
      82  
      83    VECT_VAR_DECL (buf_src2, float, 16, 8) [] = {B1, C1, A1, D1, E1, F1, G1, H1};
      84    VLOAD (vsrc, buf_src2, q, float, f, 16, 8);
      85    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
      86  
      87    if (* (uint16_t *) &vector_res != expect_alt)
      88      abort ();
      89  
      90    VECT_VAR_DECL (buf_src3, float, 16, 8) [] = {B1, C1, D1, A1, E1, F1, G1, H1};
      91    VLOAD (vsrc, buf_src3, q, float, f, 16, 8);
      92    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
      93  
      94    if (* (uint16_t *) &vector_res != expect_alt)
      95      abort ();
      96  
      97    VECT_VAR_DECL (buf_src4, float, 16, 8) [] = {B1, C1, D1, E1, A1, F1, G1, H1};
      98    VLOAD (vsrc, buf_src4, q, float, f, 16, 8);
      99    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
     100  
     101    if (* (uint16_t *) &vector_res != expect_alt)
     102      abort ();
     103  
     104    VECT_VAR_DECL (buf_src5, float, 16, 8) [] = {B1, C1, D1, E1, F1, A1, G1, H1};
     105    VLOAD (vsrc, buf_src5, q, float, f, 16, 8);
     106    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
     107  
     108    if (* (uint16_t *) &vector_res != expect_alt)
     109      abort ();
     110  
     111    VECT_VAR_DECL (buf_src6, float, 16, 8) [] = {B1, C1, D1, E1, F1, G1, A1, H1};
     112    VLOAD (vsrc, buf_src6, q, float, f, 16, 8);
     113    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
     114  
     115    if (* (uint16_t *) &vector_res != expect_alt)
     116      abort ();
     117  
     118    VECT_VAR_DECL (buf_src7, float, 16, 8) [] = {B1, C1, D1, E1, F1, G1, H1, A1};
     119    VLOAD (vsrc, buf_src7, q, float, f, 16, 8);
     120    vector_res = vmaxvq_f16 (VECT_VAR (vsrc, float, 16, 8));
     121  
     122    if (* (uint16_t *) &vector_res != expect_alt)
     123      abort ();
     124  }
     125  
     126  int
     127  main (void)
     128  {
     129    exec_vmaxv_f16 ();
     130    return 0;
     131  }