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