gcc/config/arm/arm_neon_builtins.def

   1 /* NEON builtin definitions for ARM.
   2    Copyright (C) 2013-2024 Free Software Foundation, Inc.
   3    Contributed by ARM Ltd.
   4
   5    This file is part of GCC.
   6
   7    GCC is free software; you can redistribute it and/or modify it
   8    under the terms of the GNU General Public License as published
   9    by the Free Software Foundation; either version 3, or (at your
  10    option) any later version.
  11
  12    GCC is distributed in the hope that it will be useful, but WITHOUT
  13    ANY WARRANTY; without even the implied warranty of MERCHANTABILITY
  14    or FITNESS FOR A PARTICULAR PURPOSE.  See the GNU General Public
  15    License for more details.
  16
  17    You should have received a copy of the GNU General Public License
  18    along with GCC; see the file COPYING3.  If not see
  19    <http://www.gnu.org/licenses/>.  */
  20
  21 VAR2 (BINOP, vadd, v2sf, v4sf)
  22 VAR2 (BINOP, vadd, v8hf, v4hf)
  23 VAR3 (BINOP, vaddls, v8qi, v4hi, v2si)
  24 VAR3 (BINOP, vaddlu, v8qi, v4hi, v2si)
  25 VAR3 (BINOP, vaddws, v8qi, v4hi, v2si)
  26 VAR3 (BINOP, vaddwu, v8qi, v4hi, v2si)
  27 VAR6 (BINOP, vhaddu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
  28 VAR6 (BINOP, vhadds, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
  29 VAR6 (BINOP, vrhaddu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
  30 VAR6 (BINOP, vrhadds, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
  31 VAR8 (BINOP, vqadds, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  32 VAR8 (BINOP, vqaddu, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  33 VAR3 (BINOP, vaddhn, v8hi, v4si, v2di)
  34 VAR3 (BINOP, vraddhn, v8hi, v4si, v2di)
  35 VAR2 (BINOP, vmulf, v2sf, v4sf)
  36 VAR2 (BINOP, vmulf, v8hf, v4hf)
  37 VAR2 (BINOP, vmulp, v8qi, v16qi)
  38 VAR8 (TERNOP, vmla, v8qi, v4hi, v2si, v2sf, v16qi, v8hi, v4si, v4sf)
  39 VAR3 (TERNOP, vmlals, v8qi, v4hi, v2si)
  40 VAR3 (TERNOP, vmlalu, v8qi, v4hi, v2si)
  41 VAR2 (TERNOP, vfma, v2sf, v4sf)
  42 VAR2 (TERNOP, vfma, v4hf, v8hf)
  43 VAR2 (TERNOP, vfms, v2sf, v4sf)
  44 VAR2 (TERNOP, vfms, v4hf, v8hf)
  45 VAR8 (TERNOP, vmls, v8qi, v4hi, v2si, v2sf, v16qi, v8hi, v4si, v4sf)
  46 VAR3 (TERNOP, vmlsls, v8qi, v4hi, v2si)
  47 VAR3 (TERNOP, vmlslu, v8qi, v4hi, v2si)
  48 VAR4 (BINOP, vqdmulh, v4hi, v2si, v8hi, v4si)
  49 VAR4 (BINOP, vqrdmulh, v4hi, v2si, v8hi, v4si)
  50 VAR2 (TERNOP, vqdmlal, v4hi, v2si)
  51 VAR2 (TERNOP, vqdmlsl, v4hi, v2si)
  52 VAR4 (TERNOP, vqrdmlah, v4hi, v2si, v8hi, v4si)
  53 VAR4 (TERNOP, vqrdmlsh, v4hi, v2si, v8hi, v4si)
  54 VAR2 (TERNOP, vfmal_low, v2sf, v4sf)
  55 VAR2 (TERNOP, vfmal_high, v2sf, v4sf)
  56 VAR2 (TERNOP, vfmsl_low, v2sf, v4sf)
  57 VAR2 (TERNOP, vfmsl_high, v2sf, v4sf)
  58 VAR2 (MAC_LANE, vfmal_lane_low, v2sf, v4sf)
  59 VAR1 (MAC_LANE, vfmal_lane_lowv4hf, v4sf)
  60 VAR1 (MAC_LANE, vfmal_lane_lowv8hf, v2sf)
  61 VAR2 (MAC_LANE, vfmal_lane_high, v2sf, v4sf)
  62 VAR1 (MAC_LANE, vfmal_lane_highv4hf, v4sf)
  63 VAR1 (MAC_LANE, vfmal_lane_highv8hf, v2sf)
  64 VAR2 (MAC_LANE, vfmsl_lane_low, v2sf, v4sf)
  65 VAR1 (MAC_LANE, vfmsl_lane_lowv4hf, v4sf)
  66 VAR1 (MAC_LANE, vfmsl_lane_lowv8hf, v2sf)
  67 VAR2 (MAC_LANE, vfmsl_lane_high, v2sf, v4sf)
  68 VAR1 (MAC_LANE, vfmsl_lane_highv4hf, v4sf)
  69 VAR1 (MAC_LANE, vfmsl_lane_highv8hf, v2sf)
  70 VAR3 (BINOP, vmullp, v8qi, v4hi, v2si)
  71 VAR3 (BINOP, vmulls, v8qi, v4hi, v2si)
  72 VAR3 (BINOP, vmullu, v8qi, v4hi, v2si)
  73 VAR2 (BINOP, vmulls_n, v4hi, v2si)
  74 VAR2 (BINOP, vmullu_n, v4hi, v2si)
  75 VAR2 (SETLANE, vmulls_lane, v4hi, v2si)
  76 VAR2 (SETLANE, vmullu_lane, v4hi, v2si)
  77 VAR2 (BINOP, vqdmull_n, v4hi, v2si)
  78 VAR2 (SETLANE, vqdmull_lane, v4hi, v2si)
  79 VAR4 (BINOP, vqdmulh_n, v4hi, v2si, v8hi, v4si)
  80 VAR4 (BINOP, vqrdmulh_n, v4hi, v2si, v8hi, v4si)
  81 VAR4 (SETLANE, vqdmulh_lane, v4hi, v2si, v8hi, v4si)
  82 VAR4 (SETLANE, vqrdmulh_lane, v4hi, v2si, v8hi, v4si)
  83 VAR4 (MAC_LANE, vqrdmlah_lane, v4hi, v2si, v8hi, v4si)
  84 VAR4 (MAC_LANE, vqrdmlsh_lane, v4hi, v2si, v8hi, v4si)
  85 VAR2 (BINOP, vqdmull, v4hi, v2si)
  86 VAR8 (BINOP, vshls, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  87 VAR8 (BINOP, vshlu, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  88 VAR8 (BINOP, vrshls, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  89 VAR8 (BINOP, vrshlu, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  90 VAR8 (BINOP, vqshls, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  91 VAR8 (BINOP, vqshlu, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  92 VAR8 (BINOP, vqrshls, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  93 VAR8 (BINOP, vqrshlu, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  94 VAR8 (BINOP_IMM, vshrs_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  95 VAR8 (BINOP_IMM, vshru_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  96 VAR8 (BINOP_IMM, vrshrs_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  97 VAR8 (BINOP_IMM, vrshru_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
  98 VAR3 (BINOP_IMM, vshrn_n, v8hi, v4si, v2di)
  99 VAR3 (BINOP_IMM, vrshrn_n, v8hi, v4si, v2di)
 100 VAR3 (BINOP_IMM, vqshrns_n, v8hi, v4si, v2di)
 101 VAR3 (BINOP_IMM, vqshrnu_n, v8hi, v4si, v2di)
 102 VAR3 (BINOP_IMM, vqrshrns_n, v8hi, v4si, v2di)
 103 VAR3 (BINOP_IMM, vqrshrnu_n, v8hi, v4si, v2di)
 104 VAR3 (BINOP_IMM, vqshrun_n, v8hi, v4si, v2di)
 105 VAR3 (BINOP_IMM, vqrshrun_n, v8hi, v4si, v2di)
 106 VAR8 (BINOP_IMM, vshl_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 107 VAR8 (BINOP_IMM, vqshl_s_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 108 VAR8 (BINOP_IMM, vqshl_u_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 109 VAR8 (BINOP_IMM, vqshlu_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 110 VAR3 (BINOP_IMM, vshlls_n, v8qi, v4hi, v2si)
 111 VAR3 (BINOP_IMM, vshllu_n, v8qi, v4hi, v2si)
 112 VAR8 (TERNOP_IMM, vsras_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 113 VAR8 (TERNOP_IMM, vsrau_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 114 VAR8 (TERNOP_IMM, vrsras_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 115 VAR8 (TERNOP_IMM, vrsrau_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 116 VAR2 (BINOP, vsub, v2sf, v4sf)
 117 VAR2 (BINOP, vsub, v8hf, v4hf)
 118 VAR3 (BINOP, vsubls, v8qi, v4hi, v2si)
 119 VAR3 (BINOP, vsublu, v8qi, v4hi, v2si)
 120 VAR3 (BINOP, vsubws, v8qi, v4hi, v2si)
 121 VAR3 (BINOP, vsubwu, v8qi, v4hi, v2si)
 122 VAR8 (BINOP, vqsubs, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 123 VAR8 (BINOP, vqsubu, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 124 VAR6 (BINOP, vhsubs, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 125 VAR6 (BINOP, vhsubu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 126 VAR3 (BINOP, vsubhn, v8hi, v4si, v2di)
 127 VAR3 (BINOP, vrsubhn, v8hi, v4si, v2di)
 128 VAR8 (BINOP, vceq, v8qi, v4hi, v2si, v2sf, v16qi, v8hi, v4si, v4sf)
 129 VAR2 (BINOP, vcage, v2sf, v4sf)
 130 VAR2 (BINOP, vcagt, v2sf, v4sf)
 131 VAR2 (BINOP, vcage, v4hf, v8hf)
 132 VAR2 (BINOP, vcagt, v4hf, v8hf)
 133 VAR2 (BINOP, vcale, v4hf, v8hf)
 134 VAR2 (BINOP, vcalt, v4hf, v8hf)
 135 VAR2 (BINOP, vceq, v4hf, v8hf)
 136 VAR2 (BINOP, vcge, v4hf, v8hf)
 137 VAR2 (BINOP, vcgt, v4hf, v8hf)
 138 VAR2 (BINOP, vcle, v4hf, v8hf)
 139 VAR2 (BINOP, vclt, v4hf, v8hf)
 140 VAR2 (UNOP, vceqz, v4hf, v8hf)
 141 VAR2 (UNOP, vcgez, v4hf, v8hf)
 142 VAR2 (UNOP, vcgtz, v4hf, v8hf)
 143 VAR2 (UNOP, vclez, v4hf, v8hf)
 144 VAR2 (UNOP, vcltz, v4hf, v8hf)
 145 VAR6 (BINOP, vabds, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 146 VAR6 (BINOP, vabdu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 147 VAR2 (BINOP, vabdf, v2sf, v4sf)
 148 VAR3 (BINOP, vabdls, v8qi, v4hi, v2si)
 149 VAR3 (BINOP, vabdlu, v8qi, v4hi, v2si)
 150 VAR2 (BINOP, vabd, v8hf, v4hf)
 151
 152 VAR6 (TERNOP, vabas, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 153 VAR6 (TERNOP, vabau, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 154 VAR3 (TERNOP, vabals, v8qi, v4hi, v2si)
 155 VAR3 (TERNOP, vabalu, v8qi, v4hi, v2si)
 156
 157 VAR6 (BINOP, vmaxs, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 158 VAR6 (BINOP, vmaxu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 159 VAR2 (BINOP, vmaxf, v2sf, v4sf)
 160 VAR2 (BINOP, vmaxf, v8hf, v4hf)
 161 VAR4 (BINOP, vmaxnm, v2sf, v4sf, v4hf, v8hf)
 162 VAR6 (BINOP, vmins, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 163 VAR6 (BINOP, vminu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 164 VAR2 (BINOP, vminf, v2sf, v4sf)
 165 VAR2 (BINOP, vminf, v4hf, v8hf)
 166 VAR4 (BINOP, vminnm, v2sf, v4sf, v8hf, v4hf)
 167
 168 VAR3 (BINOP, vpmaxs, v8qi, v4hi, v2si)
 169 VAR3 (BINOP, vpmaxu, v8qi, v4hi, v2si)
 170 VAR1 (BINOP, vpmaxf, v2sf)
 171 VAR1 (BINOP, vpmaxf, v4hf)
 172 VAR3 (BINOP, vpmins, v8qi, v4hi, v2si)
 173 VAR3 (BINOP, vpminu, v8qi, v4hi, v2si)
 174 VAR1 (BINOP, vpminf, v2sf)
 175 VAR1 (BINOP, vpminf, v4hf)
 176
 177 VAR4 (BINOP, vpadd, v8qi, v4hi, v2si, v2sf)
 178 VAR1 (BINOP, vpadd, v4hf)
 179 VAR6 (UNOP, vpaddls, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 180 VAR6 (UNOP, vpaddlu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 181 VAR6 (BINOP, vpadals, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 182 VAR6 (BINOP, vpadalu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 183 VAR2 (BINOP, vrecps, v2sf, v4sf)
 184 VAR2 (BINOP, vrsqrts, v2sf, v4sf)
 185 VAR2 (BINOP, vrecps, v4hf, v8hf)
 186 VAR2 (BINOP, vrsqrts, v4hf, v8hf)
 187 VAR8 (TERNOP_IMM, vsri_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 188 VAR8 (TERNOP_IMM, vsli_n, v8qi, v4hi, v2si, di, v16qi, v8hi, v4si, v2di)
 189 VAR8 (UNOP, vabs, v8qi, v4hi, v2si, v2sf, v16qi, v8hi, v4si, v4sf)
 190 VAR2 (UNOP, vabs, v8hf, v4hf)
 191 VAR2 (UNOP, vneg, v8hf, v4hf)
 192 VAR6 (UNOP, vqabs, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 193 VAR6 (UNOP, vqneg, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 194 VAR6 (UNOP, vcls, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 195 VAR6 (UNOP, vclz, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 196 VAR5 (BSWAP, bswap, v4hi, v8hi, v2si, v4si, v2di)
 197 VAR2 (UNOP, vcnt, v8qi, v16qi)
 198 VAR4 (UNOP, vrecpe, v2si, v2sf, v4si, v4sf)
 199 VAR2 (UNOP, vrecpe, v8hf, v4hf)
 200 VAR4 (UNOP, vrsqrte, v2si, v2sf, v4si, v4sf)
 201 VAR2 (UNOP, vrsqrte, v4hf, v8hf)
 202 VAR2 (UNOP, vrnd, v8hf, v4hf)
 203 VAR2 (UNOP, vrnda, v8hf, v4hf)
 204 VAR2 (UNOP, vrndm, v8hf, v4hf)
 205 VAR2 (UNOP, vrndn, v8hf, v4hf)
 206 VAR2 (UNOP, vrndp, v8hf, v4hf)
 207 VAR2 (UNOP, vrndx, v8hf, v4hf)
 208   /* FIXME: vget_lane supports more variants than this!  */
 209 VAR10 (GETLANE, vget_lane,
 210          v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di)
 211 VAR6 (GETLANE, vget_laneu, v8qi, v4hi, v2si, v16qi, v8hi, v4si)
 212 VAR10 (SETLANE, vset_lane,
 213          v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di)
 214 VAR10 (GETLANE, vdup_lane,
 215          v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di)
 216 VAR4 (GETLANE, vdup_lane, v8hf, v4hf, v8bf, v4bf)
 217 VAR7 (COMBINE, vcombine, v8qi, v4hi, v4hf, v2si, v2sf, di, v4bf)
 218 VAR7 (UNOP, vget_high, v16qi, v8hi, v8hf, v8bf, v4si, v4sf, v2di)
 219 VAR7 (UNOP, vget_low, v16qi, v8hi, v8hf, v8bf, v4si, v4sf, v2di)
 220 VAR3 (UNOP, vmovn, v8hi, v4si, v2di)
 221 VAR3 (UNOP, vqmovns, v8hi, v4si, v2di)
 222 VAR3 (UNOP, vqmovnu, v8hi, v4si, v2di)
 223 VAR3 (UNOP, vqmovun, v8hi, v4si, v2di)
 224 VAR3 (UNOP, vmovls, v8qi, v4hi, v2si)
 225 VAR3 (UNOP, vmovlu, v8qi, v4hi, v2si)
 226 VAR8 (SETLANE, vmul_lane, v4hi, v2si, v2sf, v8hi, v4si, v4sf, v4hf, v8hf)
 227 VAR6 (MAC_LANE, vmla_lane, v4hi, v2si, v2sf, v8hi, v4si, v4sf)
 228 VAR2 (MAC_LANE, vmlals_lane, v4hi, v2si)
 229 VAR2 (MAC_LANE, vmlalu_lane, v4hi, v2si)
 230 VAR2 (MAC_LANE, vqdmlal_lane, v4hi, v2si)
 231 VAR6 (MAC_LANE, vmls_lane, v4hi, v2si, v2sf, v8hi, v4si, v4sf)
 232 VAR2 (MAC_LANE, vmlsls_lane, v4hi, v2si)
 233 VAR2 (MAC_LANE, vmlslu_lane, v4hi, v2si)
 234 VAR2 (MAC_LANE, vqdmlsl_lane, v4hi, v2si)
 235 VAR8 (BINOP, vmul_n, v4hi, v2si, v2sf, v8hi, v4si, v4sf, v4hf, v8hf)
 236 VAR6 (MAC_N, vmla_n, v4hi, v2si, v2sf, v8hi, v4si, v4sf)
 237 VAR2 (MAC_N, vmlals_n, v4hi, v2si)
 238 VAR2 (MAC_N, vmlalu_n, v4hi, v2si)
 239 VAR2 (MAC_N, vqdmlal_n, v4hi, v2si)
 240 VAR6 (MAC_N, vmls_n, v4hi, v2si, v2sf, v8hi, v4si, v4sf)
 241 VAR2 (MAC_N, vmlsls_n, v4hi, v2si)
 242 VAR2 (MAC_N, vmlslu_n, v4hi, v2si)
 243 VAR2 (MAC_N, vqdmlsl_n, v4hi, v2si)
 244 VAR10 (SETLANE, vext,
 245          v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di)
 246 VAR2 (SETLANE, vext, v8hf, v4hf)
 247 VAR8 (UNOP, vrev64, v8qi, v4hi, v2si, v2sf, v16qi, v8hi, v4si, v4sf)
 248 VAR4 (UNOP, vrev32, v8qi, v4hi, v16qi, v8hi)
 249 VAR2 (UNOP, vrev16, v8qi, v16qi)
 250 VAR4 (UNOP, vcvts, v2si, v2sf, v4si, v4sf)
 251 VAR2 (UNOP, vcvts, v4hi, v8hi)
 252 VAR2 (UNOP, vcvts, v4hf, v8hf)
 253 VAR2 (UNOP, vcvtu, v4hi, v8hi)
 254 VAR2 (UNOP, vcvtu, v4hf, v8hf)
 255 VAR4 (UNOP, vcvtu, v2si, v2sf, v4si, v4sf)
 256 VAR4 (BINOP, vcvts_n, v2si, v2sf, v4si, v4sf)
 257 VAR4 (BINOP, vcvtu_n, v2si, v2sf, v4si, v4sf)
 258 VAR2 (BINOP, vcvts_n, v4hf, v8hf)
 259 VAR2 (BINOP, vcvtu_n, v4hi, v8hi)
 260 VAR2 (BINOP, vcvts_n, v4hi, v8hi)
 261 VAR2 (BINOP, vcvtu_n, v4hf, v8hf)
 262 VAR1 (UNOP, vcvtv4sf, v4hf)
 263 VAR1 (UNOP, vcvtv4hf, v4sf)
 264 VAR10 (TERNOP, vbsl,
 265          v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di)
 266 VAR2 (TERNOP, vbsl, v8hf, v4hf)
 267 VAR2 (UNOP, vrintn, v2sf, v4sf)
 268 VAR2 (UNOP, vrinta, v2sf, v4sf)
 269 VAR2 (UNOP, vrintp, v2sf, v4sf)
 270 VAR2 (UNOP, vrintm, v2sf, v4sf)
 271 VAR2 (UNOP, vrintz, v2sf, v4sf)
 272 VAR2 (UNOP, vrintx, v2sf, v4sf)
 273 VAR1 (UNOP, vcvtav2sf, v2si)
 274 VAR1 (UNOP, vcvtav4sf, v4si)
 275 VAR1 (UNOP, vcvtauv2sf, v2si)
 276 VAR1 (UNOP, vcvtauv4sf, v4si)
 277 VAR2 (UNOP, vcvtas, v4hf, v8hf)
 278 VAR2 (UNOP, vcvtau, v4hf, v8hf)
 279 VAR2 (UNOP, vcvtms, v4hf, v8hf)
 280 VAR2 (UNOP, vcvtmu, v4hf, v8hf)
 281 VAR2 (UNOP, vcvtns, v4hf, v8hf)
 282 VAR2 (UNOP, vcvtnu, v4hf, v8hf)
 283 VAR2 (UNOP, vcvtps, v4hf, v8hf)
 284 VAR2 (UNOP, vcvtpu, v4hf, v8hf)
 285 VAR1 (UNOP, vcvtpv2sf, v2si)
 286 VAR1 (UNOP, vcvtpv4sf, v4si)
 287 VAR1 (UNOP, vcvtpuv2sf, v2si)
 288 VAR1 (UNOP, vcvtpuv4sf, v4si)
 289 VAR1 (UNOP, vcvtmv2sf, v2si)
 290 VAR1 (UNOP, vcvtmv4sf, v4si)
 291 VAR1 (UNOP, vcvtmuv2sf, v2si)
 292 VAR1 (UNOP, vcvtmuv4sf, v4si)
 293 VAR1 (COMBINE, vtbl1, v8qi)
 294 VAR1 (COMBINE, vtbl2, v8qi)
 295 VAR1 (COMBINE, vtbl3, v8qi)
 296 VAR1 (COMBINE, vtbl4, v8qi)
 297 VAR1 (TERNOP, vtbx1, v8qi)
 298 VAR1 (TERNOP, vtbx2, v8qi)
 299 VAR1 (TERNOP, vtbx3, v8qi)
 300 VAR1 (TERNOP, vtbx4, v8qi)
 301 VAR13 (LOAD1, vld1,
 302         v8qi, v4hi, v4hf, v2si, v2sf, v16qi, v8hi, v8hf, v4si, v4sf, v2di,
 303         v4bf, v8bf)
 304 VAR7 (LOAD1, vld1_x2, v8qi, v4hi, v2si, di, v4hf, v2sf, v4bf)
 305 VAR7 (LOAD1, vld1q_x2, v16qi, v8hi, v4si, v2di, v8hf, v4sf, v8bf)
 306 VAR7 (LOAD1, vld1_x3, v8qi, v4hi, v2si, di, v4hf, v2sf, v4bf)
 307 VAR7 (LOAD1, vld1q_x3, v16qi, v8hi, v4si, v2di, v8hf, v4sf, v8bf)
 308 VAR7 (LOAD1, vld1_x4, v8qi, v4hi, v2si, di, v4hf, v2sf, v4bf)
 309 VAR7 (LOAD1, vld1q_x4, v16qi, v8hi, v4si, v2di, v8hf, v4sf, v8bf)
 310 VAR12 (LOAD1LANE, vld1_lane,
 311         v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di, v4bf, v8bf)
 312 VAR10 (LOAD1, vld1_dup,
 313         v8qi, v4hi, v2si, v2sf, di, v16qi, v8hi, v4si, v4sf, v2di)
 314 VAR14 (STORE1, vst1,
 315         v8qi, v4hi, v4hf, v2si, v2sf, di, v16qi, v8hi, v8hf, v4si, v4sf, v2di,
 316         v4bf, v8bf)
 317 VAR7 (STORE1, vst1_x2, v8qi, v4hi, v2si, di, v4hf, v2sf, v4bf)
 318 VAR7 (STORE1, vst1q_x2, v16qi, v8hi, v4si, v2di, v8hf, v4sf, v8bf)
 319 VAR7 (STORE1, vst1_x3, v8qi, v4hi, v2si, di, v4hf, v2sf, v4bf)
 320 VAR7 (STORE1, vst1q_x3, v16qi, v8hi, v4si, v2di, v8hf, v4sf, v8bf)
 321 VAR7 (STORE1, vst1_x4, v8qi, v4hi, v2si, di, v4hf, v2sf, v4bf)
 322 VAR7 (STORE1, vst1q_x4, v16qi, v8hi, v4si, v2di, v8hf, v4sf, v8bf)
 323 VAR14 (STORE1LANE, vst1_lane,
 324        v8qi, v4hi, v4hf, v2si, v2sf, di, v16qi, v8hi, v8hf, v4si, v4sf, v2di, v4bf, v8bf)
 325 VAR13 (LOAD1, vld2,
 326         v8qi, v4hi, v4hf, v2si, v2sf, di, v16qi, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 327 VAR11 (LOAD1LANE, vld2_lane,
 328        v8qi, v4hi, v4hf, v2si, v2sf, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 329 VAR8 (LOAD1, vld2_dup, v8qi, v4hi, v4hf, v2si, v2sf, di, v4bf, v8bf)
 330 VAR13 (STORE1, vst2,
 331         v8qi, v4hi, v4hf, v4bf, v2si, v2sf, di, v16qi, v8hi, v8hf, v8bf, v4si, v4sf)
 332 VAR11 (STORE1LANE, vst2_lane,
 333         v8qi, v4hi, v4hf, v2si, v2sf, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 334 VAR13 (LOAD1, vld3,
 335         v8qi, v4hi, v4hf, v2si, v2sf, di, v16qi, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 336 VAR11 (LOAD1LANE, vld3_lane,
 337         v8qi, v4hi, v4hf, v2si, v2sf, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 338 VAR8 (LOAD1, vld3_dup, v8qi, v4hi, v4hf, v2si, v2sf, di, v4bf, v8bf)
 339 VAR13 (STORE1, vst3,
 340         v8qi, v4hi, v4hf, v4bf, v2si, v2sf, di, v16qi, v8hi, v8hf, v8bf, v4si, v4sf)
 341 VAR11 (STORE1LANE, vst3_lane,
 342         v8qi, v4hi, v4hf, v2si, v2sf, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 343 VAR13 (LOAD1, vld4,
 344         v8qi, v4hi, v4hf, v2si, v2sf, di, v16qi, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 345 VAR11 (LOAD1LANE, vld4_lane,
 346         v8qi, v4hi, v4hf, v2si, v2sf, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 347 VAR8 (LOAD1, vld4_dup, v8qi, v4hi, v4hf, v2si, v2sf, di, v4bf, v8bf)
 348 VAR13 (STORE1, vst4,
 349         v8qi, v4hi, v4hf, v4bf, v2si, v2sf, di, v16qi, v8hi, v8hf, v8bf, v4si, v4sf)
 350 VAR11 (STORE1LANE, vst4_lane,
 351         v8qi, v4hi, v4hf, v2si, v2sf, v8hi, v8hf, v4si, v4sf, v4bf, v8bf)
 352 VAR2 (TERNOP, sdot, v8qi, v16qi)
 353 VAR2 (UTERNOP, udot, v8qi, v16qi)
 354 VAR2 (MAC_LANE, sdot_lane, v8qi, v16qi)
 355 VAR2 (UMAC_LANE, udot_lane, v8qi, v16qi)
 356 VAR2 (MAC_LANE, sdot_laneq, v8qi, v16qi)
 357 VAR2 (UMAC_LANE, udot_laneq, v8qi, v16qi)
 358
 359 VAR2 (USTERNOP, usdot, v8qi, v16qi)
 360 VAR2 (USMAC_LANE_QUADTUP, usdot_lane, v8qi, v16qi)
 361 VAR2 (SUMAC_LANE_QUADTUP, sudot_lane, v8qi, v16qi)
 362 VAR2 (USMAC_LANE_QUADTUP, usdot_laneq, v8qi, v16qi)
 363 VAR2 (SUMAC_LANE_QUADTUP, sudot_laneq, v8qi, v16qi)
 364
 365 VAR4 (BINOP, vcadd90, v4hf, v2sf, v8hf, v4sf)
 366 VAR4 (BINOP, vcadd270, v4hf, v2sf, v8hf, v4sf)
 367 VAR4 (TERNOP, vcmla0, v2sf, v4sf, v4hf, v8hf)
 368 VAR4 (TERNOP, vcmla90, v2sf, v4sf, v4hf, v8hf)
 369 VAR4 (TERNOP, vcmla180, v2sf, v4sf, v4hf, v8hf)
 370 VAR4 (TERNOP, vcmla270, v2sf, v4sf, v4hf, v8hf)
 371
 372 VAR4 (MAC_LANE_PAIR, vcmla_lane0, v2sf, v4hf, v8hf, v4sf)
 373 VAR4 (MAC_LANE_PAIR, vcmla_lane90, v2sf, v4hf, v8hf, v4sf)
 374 VAR4 (MAC_LANE_PAIR, vcmla_lane180, v2sf, v4hf, v8hf, v4sf)
 375 VAR4 (MAC_LANE_PAIR, vcmla_lane270, v2sf, v4hf, v8hf, v4sf)
 376
 377 VAR2 (MAC_LANE_PAIR, vcmla_laneq0, v2sf, v4hf)
 378 VAR2 (MAC_LANE_PAIR, vcmla_laneq90, v2sf, v4hf)
 379 VAR2 (MAC_LANE_PAIR, vcmla_laneq180, v2sf, v4hf)
 380 VAR2 (MAC_LANE_PAIR, vcmla_laneq270, v2sf, v4hf)
 381
 382 VAR2 (MAC_LANE_PAIR, vcmlaq_lane0, v4sf, v8hf)
 383 VAR2 (MAC_LANE_PAIR, vcmlaq_lane90, v4sf, v8hf)
 384 VAR2 (MAC_LANE_PAIR, vcmlaq_lane180, v4sf, v8hf)
 385 VAR2 (MAC_LANE_PAIR, vcmlaq_lane270, v4sf, v8hf)
 386
 387 VAR1 (TERNOP, smmla, v16qi)
 388 VAR1 (UTERNOP, ummla, v16qi)
 389 VAR1 (USTERNOP, usmmla, v16qi)
 390
 391 VAR2 (TERNOP, vbfdot, v2sf, v4sf)
 392 VAR2 (MAC_LANE_PAIR, vbfdot_lanev4bf, v2sf, v4sf)
 393 VAR2 (MAC_LANE_PAIR, vbfdot_lanev8bf, v2sf, v4sf)
 394
 395 VAR2 (UNOP, vbfcvt, sf, bf)
 396 VAR2 (UNOP, vbfcvt, v4bf, v8bf)
 397 VAR1 (UNOP, vbfcvt_high, v8bf)
 398 VAR2 (UNOP, vbfcvtv4sf, v4bf, v8bf)
 399 VAR1 (BINOP, vbfcvtv4sf_high, v8bf)
 400
 401 VAR1 (TERNOP, vmmla, v8bf)
 402
 403 VAR1 (TERNOP, vfmab, v8bf)
 404 VAR1 (TERNOP, vfmat, v8bf)
 405 VAR1 (MAC_LANE, vfmab_lane, v8bf)
 406 VAR1 (MAC_LANE, vfmat_lane, v8bf)
 407 VAR1 (MAC_LANE, vfmab_laneq, v8bf)
 408 VAR1 (MAC_LANE, vfmat_laneq, v8bf)