1  #include <arm_neon.h>
       2  #include "arm-neon-ref.h"
       3  #include "compute-ref-data.h"
       4  
       5  /* Expected results splitted in several chunks.  */
       6  /* Chunk 0.  */
       7  VECT_VAR_DECL(expected0,int,8,8) [] = { 0xf0, 0xf1, 0xf2, 0xf3,
       8  					0xf4, 0xf5, 0xf6, 0xf7 };
       9  VECT_VAR_DECL(expected0,int,16,4) [] = { 0xfff0, 0xfff1,
      10  					 0xfff2, 0xfff3 };
      11  VECT_VAR_DECL(expected0,int,32,2) [] = { 0xfffffff0, 0xfffffff1 };
      12  VECT_VAR_DECL(expected0,uint,8,8) [] = { 0xf0, 0xf1, 0xf2, 0xf3,
      13  					 0xf4, 0xf5, 0xf6, 0xf7 };
      14  VECT_VAR_DECL(expected0,uint,16,4) [] = { 0xfff0, 0xfff1,
      15  					  0xfff2, 0xfff3 };
      16  VECT_VAR_DECL(expected0,uint,32,2) [] = { 0xfffffff0,
      17  					  0xfffffff1 };
      18  VECT_VAR_DECL(expected0,poly,8,8) [] = { 0xf0, 0xf1, 0xf2, 0xf3,
      19  					 0xf4, 0xf5, 0xf6, 0xf7 };
      20  VECT_VAR_DECL(expected0,poly,16,4) [] = { 0xfff0, 0xfff1,
      21  					  0xfff2, 0xfff3 };
      22  #if defined (FP16_SUPPORTED)
      23  VECT_VAR_DECL (expected0, hfloat, 16, 4) [] = { 0xcc00, 0xcb80,
      24  						0xcb00, 0xca80 };
      25  #endif
      26  VECT_VAR_DECL(expected0,hfloat,32,2) [] = { 0xc1800000, 0xc1700000 };
      27  VECT_VAR_DECL(expected0,int,8,16) [] = { 0xf0, 0xf1, 0xf2, 0xf3,
      28  					 0xf4, 0xf5, 0xf6, 0xf7,
      29  					 0xf8, 0xf9, 0xfa, 0xfb,
      30  					 0xfc, 0xfd, 0xfe, 0xff };
      31  VECT_VAR_DECL(expected0,int,16,8) [] = { 0xfff0, 0xfff1,
      32  					 0xfff2, 0xfff3,
      33  					 0xfff4, 0xfff5,
      34  					 0xfff6, 0xfff7 };
      35  VECT_VAR_DECL(expected0,int,32,4) [] = { 0xfffffff0, 0xfffffff1,
      36  					 0xfffffff2, 0xfffffff3 };
      37  VECT_VAR_DECL(expected0,uint,8,16) [] = { 0xf0, 0xf1, 0xf2, 0xf3,
      38  					  0xf4, 0xf5, 0xf6, 0xf7,
      39  					  0xf8, 0xf9, 0xfa, 0xfb,
      40  					  0xfc, 0xfd, 0xfe, 0xff };
      41  VECT_VAR_DECL(expected0,uint,16,8) [] = { 0xfff0, 0xfff1,
      42  					  0xfff2, 0xfff3,
      43  					  0xfff4, 0xfff5,
      44  					  0xfff6, 0xfff7 };
      45  VECT_VAR_DECL(expected0,uint,32,4) [] = { 0xfffffff0, 0xfffffff1,
      46  					  0xfffffff2, 0xfffffff3 };
      47  VECT_VAR_DECL(expected0,poly,8,16) [] = { 0xf0, 0xf1, 0xf2, 0xf3,
      48  					  0xf4, 0xf5, 0xf6, 0xf7,
      49  					  0xf8, 0xf9, 0xfa, 0xfb,
      50  					  0xfc, 0xfd, 0xfe, 0xff };
      51  VECT_VAR_DECL(expected0,poly,16,8) [] = { 0xfff0, 0xfff1,
      52  					  0xfff2, 0xfff3,
      53  					  0xfff4, 0xfff5,
      54  					  0xfff6, 0xfff7 };
      55  #if defined (FP16_SUPPORTED)
      56  VECT_VAR_DECL (expected0, hfloat, 16, 8) [] = { 0xcc00, 0xcb80,
      57  						0xcb00, 0xca80,
      58  						0xca00, 0xc980,
      59  						0xc900, 0xc880 };
      60  #endif
      61  VECT_VAR_DECL(expected0,hfloat,32,4) [] = { 0xc1800000, 0xc1700000,
      62  					    0xc1600000, 0xc1500000 };
      63  
      64  /* Chunk 1.  */
      65  VECT_VAR_DECL(expected1,int,8,8) [] = { 0x11, 0x11, 0x11, 0x11,
      66  					0x11, 0x11, 0x11, 0x11 };
      67  VECT_VAR_DECL(expected1,int,16,4) [] = { 0x22, 0x22, 0x22, 0x22 };
      68  VECT_VAR_DECL(expected1,int,32,2) [] = { 0x33, 0x33 };
      69  VECT_VAR_DECL(expected1,uint,8,8) [] = { 0x55, 0x55, 0x55, 0x55,
      70  					 0x55, 0x55, 0x55, 0x55 };
      71  VECT_VAR_DECL(expected1,uint,16,4) [] = { 0x66, 0x66, 0x66, 0x66 };
      72  VECT_VAR_DECL(expected1,uint,32,2) [] = { 0x77, 0x77 };
      73  VECT_VAR_DECL(expected1,poly,8,8) [] = { 0x55, 0x55, 0x55, 0x55,
      74  					 0x55, 0x55, 0x55, 0x55 };
      75  VECT_VAR_DECL(expected1,poly,16,4) [] = { 0x66, 0x66, 0x66, 0x66 };
      76  #if defined (FP16_SUPPORTED)
      77  VECT_VAR_DECL (expected1, hfloat, 16, 4) [] = { 0x4b4d, 0x4b4d,
      78  						0x4b4d, 0x4b4d };
      79  #endif
      80  VECT_VAR_DECL(expected1,hfloat,32,2) [] = { 0x42066666, 0x42066666 };
      81  VECT_VAR_DECL(expected1,int,8,16) [] = { 0x11, 0x11, 0x11, 0x11,
      82  					 0x11, 0x11, 0x11, 0x11,
      83  					 0x11, 0x11, 0x11, 0x11,
      84  					 0x11, 0x11, 0x11, 0x11 };
      85  VECT_VAR_DECL(expected1,int,16,8) [] = { 0x22, 0x22, 0x22, 0x22,
      86  					 0x22, 0x22, 0x22, 0x22 };
      87  VECT_VAR_DECL(expected1,int,32,4) [] = { 0x33, 0x33, 0x33, 0x33 };
      88  VECT_VAR_DECL(expected1,uint,8,16) [] = { 0x55, 0x55, 0x55, 0x55,
      89  					  0x55, 0x55, 0x55, 0x55,
      90  					  0x55, 0x55, 0x55, 0x55,
      91  					  0x55, 0x55, 0x55, 0x55 };
      92  VECT_VAR_DECL(expected1,uint,16,8) [] = { 0x66, 0x66, 0x66, 0x66,
      93  					  0x66, 0x66, 0x66, 0x66 };
      94  VECT_VAR_DECL(expected1,uint,32,4) [] = { 0x77, 0x77, 0x77, 0x77 };
      95  VECT_VAR_DECL(expected1,poly,8,16) [] = { 0x55, 0x55, 0x55, 0x55,
      96  					  0x55, 0x55, 0x55, 0x55,
      97  					  0x55, 0x55, 0x55, 0x55,
      98  					  0x55, 0x55, 0x55, 0x55 };
      99  VECT_VAR_DECL(expected1,poly,16,8) [] = { 0x66, 0x66, 0x66, 0x66,
     100  					  0x66, 0x66, 0x66, 0x66 };
     101  #if defined (FP16_SUPPORTED)
     102  VECT_VAR_DECL (expected1, hfloat, 16, 8) [] = { 0x4b4d, 0x4b4d,
     103  						0x4b4d, 0x4b4d,
     104  						0x4b4d, 0x4b4d,
     105  						0x4b4d, 0x4b4d };
     106  #endif
     107  VECT_VAR_DECL(expected1,hfloat,32,4) [] = { 0x42073333, 0x42073333,
     108  					    0x42073333, 0x42073333 };
     109  
     110  #define INSN_NAME vuzp
     111  #define TEST_MSG "VUZP/VUZPQ"
     112  
     113  #include "vshuffle.inc"