Lines Matching refs:NEON
5200 { #NameBase, NEON::BI__builtin_neon_ ## NameBase, 0, 0, 0 }
5203 { #NameBase, NEON:: BI__builtin_neon_ ## NameBase, \
5207 { #NameBase, NEON:: BI__builtin_neon_ ## NameBase, \
6021 case NEON::BI__builtin_neon_vcled_s64: in EmitCommonNeonSISDBuiltinExpr()
6022 case NEON::BI__builtin_neon_vcled_u64: in EmitCommonNeonSISDBuiltinExpr()
6023 case NEON::BI__builtin_neon_vcles_f32: in EmitCommonNeonSISDBuiltinExpr()
6024 case NEON::BI__builtin_neon_vcled_f64: in EmitCommonNeonSISDBuiltinExpr()
6025 case NEON::BI__builtin_neon_vcltd_s64: in EmitCommonNeonSISDBuiltinExpr()
6026 case NEON::BI__builtin_neon_vcltd_u64: in EmitCommonNeonSISDBuiltinExpr()
6027 case NEON::BI__builtin_neon_vclts_f32: in EmitCommonNeonSISDBuiltinExpr()
6028 case NEON::BI__builtin_neon_vcltd_f64: in EmitCommonNeonSISDBuiltinExpr()
6029 case NEON::BI__builtin_neon_vcales_f32: in EmitCommonNeonSISDBuiltinExpr()
6030 case NEON::BI__builtin_neon_vcaled_f64: in EmitCommonNeonSISDBuiltinExpr()
6031 case NEON::BI__builtin_neon_vcalts_f32: in EmitCommonNeonSISDBuiltinExpr()
6032 case NEON::BI__builtin_neon_vcaltd_f64: in EmitCommonNeonSISDBuiltinExpr()
6110 case NEON::BI__builtin_neon_splat_lane_v: in EmitCommonNeonBuiltinExpr()
6111 case NEON::BI__builtin_neon_splat_laneq_v: in EmitCommonNeonBuiltinExpr()
6112 case NEON::BI__builtin_neon_splatq_lane_v: in EmitCommonNeonBuiltinExpr()
6113 case NEON::BI__builtin_neon_splatq_laneq_v: { in EmitCommonNeonBuiltinExpr()
6115 if (BuiltinID == NEON::BI__builtin_neon_splatq_lane_v) in EmitCommonNeonBuiltinExpr()
6117 if (BuiltinID == NEON::BI__builtin_neon_splat_laneq_v) in EmitCommonNeonBuiltinExpr()
6123 case NEON::BI__builtin_neon_vpadd_v: in EmitCommonNeonBuiltinExpr()
6124 case NEON::BI__builtin_neon_vpaddq_v: in EmitCommonNeonBuiltinExpr()
6130 case NEON::BI__builtin_neon_vabs_v: in EmitCommonNeonBuiltinExpr()
6131 case NEON::BI__builtin_neon_vabsq_v: in EmitCommonNeonBuiltinExpr()
6135 case NEON::BI__builtin_neon_vaddhn_v: { in EmitCommonNeonBuiltinExpr()
6152 case NEON::BI__builtin_neon_vcale_v: in EmitCommonNeonBuiltinExpr()
6153 case NEON::BI__builtin_neon_vcaleq_v: in EmitCommonNeonBuiltinExpr()
6154 case NEON::BI__builtin_neon_vcalt_v: in EmitCommonNeonBuiltinExpr()
6155 case NEON::BI__builtin_neon_vcaltq_v: in EmitCommonNeonBuiltinExpr()
6158 case NEON::BI__builtin_neon_vcage_v: in EmitCommonNeonBuiltinExpr()
6159 case NEON::BI__builtin_neon_vcageq_v: in EmitCommonNeonBuiltinExpr()
6160 case NEON::BI__builtin_neon_vcagt_v: in EmitCommonNeonBuiltinExpr()
6161 case NEON::BI__builtin_neon_vcagtq_v: { in EmitCommonNeonBuiltinExpr()
6180 case NEON::BI__builtin_neon_vceqz_v: in EmitCommonNeonBuiltinExpr()
6181 case NEON::BI__builtin_neon_vceqzq_v: in EmitCommonNeonBuiltinExpr()
6184 case NEON::BI__builtin_neon_vcgez_v: in EmitCommonNeonBuiltinExpr()
6185 case NEON::BI__builtin_neon_vcgezq_v: in EmitCommonNeonBuiltinExpr()
6188 case NEON::BI__builtin_neon_vclez_v: in EmitCommonNeonBuiltinExpr()
6189 case NEON::BI__builtin_neon_vclezq_v: in EmitCommonNeonBuiltinExpr()
6192 case NEON::BI__builtin_neon_vcgtz_v: in EmitCommonNeonBuiltinExpr()
6193 case NEON::BI__builtin_neon_vcgtzq_v: in EmitCommonNeonBuiltinExpr()
6196 case NEON::BI__builtin_neon_vcltz_v: in EmitCommonNeonBuiltinExpr()
6197 case NEON::BI__builtin_neon_vcltzq_v: in EmitCommonNeonBuiltinExpr()
6200 case NEON::BI__builtin_neon_vclz_v: in EmitCommonNeonBuiltinExpr()
6201 case NEON::BI__builtin_neon_vclzq_v: in EmitCommonNeonBuiltinExpr()
6206 case NEON::BI__builtin_neon_vcvt_f32_v: in EmitCommonNeonBuiltinExpr()
6207 case NEON::BI__builtin_neon_vcvtq_f32_v: in EmitCommonNeonBuiltinExpr()
6213 case NEON::BI__builtin_neon_vcvt_f16_v: in EmitCommonNeonBuiltinExpr()
6214 case NEON::BI__builtin_neon_vcvtq_f16_v: in EmitCommonNeonBuiltinExpr()
6220 case NEON::BI__builtin_neon_vcvt_n_f16_v: in EmitCommonNeonBuiltinExpr()
6221 case NEON::BI__builtin_neon_vcvt_n_f32_v: in EmitCommonNeonBuiltinExpr()
6222 case NEON::BI__builtin_neon_vcvt_n_f64_v: in EmitCommonNeonBuiltinExpr()
6223 case NEON::BI__builtin_neon_vcvtq_n_f16_v: in EmitCommonNeonBuiltinExpr()
6224 case NEON::BI__builtin_neon_vcvtq_n_f32_v: in EmitCommonNeonBuiltinExpr()
6225 case NEON::BI__builtin_neon_vcvtq_n_f64_v: { in EmitCommonNeonBuiltinExpr()
6231 case NEON::BI__builtin_neon_vcvt_n_s16_v: in EmitCommonNeonBuiltinExpr()
6232 case NEON::BI__builtin_neon_vcvt_n_s32_v: in EmitCommonNeonBuiltinExpr()
6233 case NEON::BI__builtin_neon_vcvt_n_u16_v: in EmitCommonNeonBuiltinExpr()
6234 case NEON::BI__builtin_neon_vcvt_n_u32_v: in EmitCommonNeonBuiltinExpr()
6235 case NEON::BI__builtin_neon_vcvt_n_s64_v: in EmitCommonNeonBuiltinExpr()
6236 case NEON::BI__builtin_neon_vcvt_n_u64_v: in EmitCommonNeonBuiltinExpr()
6237 case NEON::BI__builtin_neon_vcvtq_n_s16_v: in EmitCommonNeonBuiltinExpr()
6238 case NEON::BI__builtin_neon_vcvtq_n_s32_v: in EmitCommonNeonBuiltinExpr()
6239 case NEON::BI__builtin_neon_vcvtq_n_u16_v: in EmitCommonNeonBuiltinExpr()
6240 case NEON::BI__builtin_neon_vcvtq_n_u32_v: in EmitCommonNeonBuiltinExpr()
6241 case NEON::BI__builtin_neon_vcvtq_n_s64_v: in EmitCommonNeonBuiltinExpr()
6242 case NEON::BI__builtin_neon_vcvtq_n_u64_v: { in EmitCommonNeonBuiltinExpr()
6247 case NEON::BI__builtin_neon_vcvt_s32_v: in EmitCommonNeonBuiltinExpr()
6248 case NEON::BI__builtin_neon_vcvt_u32_v: in EmitCommonNeonBuiltinExpr()
6249 case NEON::BI__builtin_neon_vcvt_s64_v: in EmitCommonNeonBuiltinExpr()
6250 case NEON::BI__builtin_neon_vcvt_u64_v: in EmitCommonNeonBuiltinExpr()
6251 case NEON::BI__builtin_neon_vcvt_s16_v: in EmitCommonNeonBuiltinExpr()
6252 case NEON::BI__builtin_neon_vcvt_u16_v: in EmitCommonNeonBuiltinExpr()
6253 case NEON::BI__builtin_neon_vcvtq_s32_v: in EmitCommonNeonBuiltinExpr()
6254 case NEON::BI__builtin_neon_vcvtq_u32_v: in EmitCommonNeonBuiltinExpr()
6255 case NEON::BI__builtin_neon_vcvtq_s64_v: in EmitCommonNeonBuiltinExpr()
6256 case NEON::BI__builtin_neon_vcvtq_u64_v: in EmitCommonNeonBuiltinExpr()
6257 case NEON::BI__builtin_neon_vcvtq_s16_v: in EmitCommonNeonBuiltinExpr()
6258 case NEON::BI__builtin_neon_vcvtq_u16_v: { in EmitCommonNeonBuiltinExpr()
6263 case NEON::BI__builtin_neon_vcvta_s16_v: in EmitCommonNeonBuiltinExpr()
6264 case NEON::BI__builtin_neon_vcvta_s32_v: in EmitCommonNeonBuiltinExpr()
6265 case NEON::BI__builtin_neon_vcvta_s64_v: in EmitCommonNeonBuiltinExpr()
6266 case NEON::BI__builtin_neon_vcvta_u16_v: in EmitCommonNeonBuiltinExpr()
6267 case NEON::BI__builtin_neon_vcvta_u32_v: in EmitCommonNeonBuiltinExpr()
6268 case NEON::BI__builtin_neon_vcvta_u64_v: in EmitCommonNeonBuiltinExpr()
6269 case NEON::BI__builtin_neon_vcvtaq_s16_v: in EmitCommonNeonBuiltinExpr()
6270 case NEON::BI__builtin_neon_vcvtaq_s32_v: in EmitCommonNeonBuiltinExpr()
6271 case NEON::BI__builtin_neon_vcvtaq_s64_v: in EmitCommonNeonBuiltinExpr()
6272 case NEON::BI__builtin_neon_vcvtaq_u16_v: in EmitCommonNeonBuiltinExpr()
6273 case NEON::BI__builtin_neon_vcvtaq_u32_v: in EmitCommonNeonBuiltinExpr()
6274 case NEON::BI__builtin_neon_vcvtaq_u64_v: in EmitCommonNeonBuiltinExpr()
6275 case NEON::BI__builtin_neon_vcvtn_s16_v: in EmitCommonNeonBuiltinExpr()
6276 case NEON::BI__builtin_neon_vcvtn_s32_v: in EmitCommonNeonBuiltinExpr()
6277 case NEON::BI__builtin_neon_vcvtn_s64_v: in EmitCommonNeonBuiltinExpr()
6278 case NEON::BI__builtin_neon_vcvtn_u16_v: in EmitCommonNeonBuiltinExpr()
6279 case NEON::BI__builtin_neon_vcvtn_u32_v: in EmitCommonNeonBuiltinExpr()
6280 case NEON::BI__builtin_neon_vcvtn_u64_v: in EmitCommonNeonBuiltinExpr()
6281 case NEON::BI__builtin_neon_vcvtnq_s16_v: in EmitCommonNeonBuiltinExpr()
6282 case NEON::BI__builtin_neon_vcvtnq_s32_v: in EmitCommonNeonBuiltinExpr()
6283 case NEON::BI__builtin_neon_vcvtnq_s64_v: in EmitCommonNeonBuiltinExpr()
6284 case NEON::BI__builtin_neon_vcvtnq_u16_v: in EmitCommonNeonBuiltinExpr()
6285 case NEON::BI__builtin_neon_vcvtnq_u32_v: in EmitCommonNeonBuiltinExpr()
6286 case NEON::BI__builtin_neon_vcvtnq_u64_v: in EmitCommonNeonBuiltinExpr()
6287 case NEON::BI__builtin_neon_vcvtp_s16_v: in EmitCommonNeonBuiltinExpr()
6288 case NEON::BI__builtin_neon_vcvtp_s32_v: in EmitCommonNeonBuiltinExpr()
6289 case NEON::BI__builtin_neon_vcvtp_s64_v: in EmitCommonNeonBuiltinExpr()
6290 case NEON::BI__builtin_neon_vcvtp_u16_v: in EmitCommonNeonBuiltinExpr()
6291 case NEON::BI__builtin_neon_vcvtp_u32_v: in EmitCommonNeonBuiltinExpr()
6292 case NEON::BI__builtin_neon_vcvtp_u64_v: in EmitCommonNeonBuiltinExpr()
6293 case NEON::BI__builtin_neon_vcvtpq_s16_v: in EmitCommonNeonBuiltinExpr()
6294 case NEON::BI__builtin_neon_vcvtpq_s32_v: in EmitCommonNeonBuiltinExpr()
6295 case NEON::BI__builtin_neon_vcvtpq_s64_v: in EmitCommonNeonBuiltinExpr()
6296 case NEON::BI__builtin_neon_vcvtpq_u16_v: in EmitCommonNeonBuiltinExpr()
6297 case NEON::BI__builtin_neon_vcvtpq_u32_v: in EmitCommonNeonBuiltinExpr()
6298 case NEON::BI__builtin_neon_vcvtpq_u64_v: in EmitCommonNeonBuiltinExpr()
6299 case NEON::BI__builtin_neon_vcvtm_s16_v: in EmitCommonNeonBuiltinExpr()
6300 case NEON::BI__builtin_neon_vcvtm_s32_v: in EmitCommonNeonBuiltinExpr()
6301 case NEON::BI__builtin_neon_vcvtm_s64_v: in EmitCommonNeonBuiltinExpr()
6302 case NEON::BI__builtin_neon_vcvtm_u16_v: in EmitCommonNeonBuiltinExpr()
6303 case NEON::BI__builtin_neon_vcvtm_u32_v: in EmitCommonNeonBuiltinExpr()
6304 case NEON::BI__builtin_neon_vcvtm_u64_v: in EmitCommonNeonBuiltinExpr()
6305 case NEON::BI__builtin_neon_vcvtmq_s16_v: in EmitCommonNeonBuiltinExpr()
6306 case NEON::BI__builtin_neon_vcvtmq_s32_v: in EmitCommonNeonBuiltinExpr()
6307 case NEON::BI__builtin_neon_vcvtmq_s64_v: in EmitCommonNeonBuiltinExpr()
6308 case NEON::BI__builtin_neon_vcvtmq_u16_v: in EmitCommonNeonBuiltinExpr()
6309 case NEON::BI__builtin_neon_vcvtmq_u32_v: in EmitCommonNeonBuiltinExpr()
6310 case NEON::BI__builtin_neon_vcvtmq_u64_v: { in EmitCommonNeonBuiltinExpr()
6314 case NEON::BI__builtin_neon_vcvtx_f32_v: { in EmitCommonNeonBuiltinExpr()
6319 case NEON::BI__builtin_neon_vext_v: in EmitCommonNeonBuiltinExpr()
6320 case NEON::BI__builtin_neon_vextq_v: { in EmitCommonNeonBuiltinExpr()
6330 case NEON::BI__builtin_neon_vfma_v: in EmitCommonNeonBuiltinExpr()
6331 case NEON::BI__builtin_neon_vfmaq_v: { in EmitCommonNeonBuiltinExpr()
6341 case NEON::BI__builtin_neon_vld1_v: in EmitCommonNeonBuiltinExpr()
6342 case NEON::BI__builtin_neon_vld1q_v: { in EmitCommonNeonBuiltinExpr()
6347 case NEON::BI__builtin_neon_vld1_x2_v: in EmitCommonNeonBuiltinExpr()
6348 case NEON::BI__builtin_neon_vld1q_x2_v: in EmitCommonNeonBuiltinExpr()
6349 case NEON::BI__builtin_neon_vld1_x3_v: in EmitCommonNeonBuiltinExpr()
6350 case NEON::BI__builtin_neon_vld1q_x3_v: in EmitCommonNeonBuiltinExpr()
6351 case NEON::BI__builtin_neon_vld1_x4_v: in EmitCommonNeonBuiltinExpr()
6352 case NEON::BI__builtin_neon_vld1q_x4_v: { in EmitCommonNeonBuiltinExpr()
6362 case NEON::BI__builtin_neon_vld2_v: in EmitCommonNeonBuiltinExpr()
6363 case NEON::BI__builtin_neon_vld2q_v: in EmitCommonNeonBuiltinExpr()
6364 case NEON::BI__builtin_neon_vld3_v: in EmitCommonNeonBuiltinExpr()
6365 case NEON::BI__builtin_neon_vld3q_v: in EmitCommonNeonBuiltinExpr()
6366 case NEON::BI__builtin_neon_vld4_v: in EmitCommonNeonBuiltinExpr()
6367 case NEON::BI__builtin_neon_vld4q_v: in EmitCommonNeonBuiltinExpr()
6368 case NEON::BI__builtin_neon_vld2_dup_v: in EmitCommonNeonBuiltinExpr()
6369 case NEON::BI__builtin_neon_vld2q_dup_v: in EmitCommonNeonBuiltinExpr()
6370 case NEON::BI__builtin_neon_vld3_dup_v: in EmitCommonNeonBuiltinExpr()
6371 case NEON::BI__builtin_neon_vld3q_dup_v: in EmitCommonNeonBuiltinExpr()
6372 case NEON::BI__builtin_neon_vld4_dup_v: in EmitCommonNeonBuiltinExpr()
6373 case NEON::BI__builtin_neon_vld4q_dup_v: { in EmitCommonNeonBuiltinExpr()
6382 case NEON::BI__builtin_neon_vld1_dup_v: in EmitCommonNeonBuiltinExpr()
6383 case NEON::BI__builtin_neon_vld1q_dup_v: { in EmitCommonNeonBuiltinExpr()
6392 case NEON::BI__builtin_neon_vld2_lane_v: in EmitCommonNeonBuiltinExpr()
6393 case NEON::BI__builtin_neon_vld2q_lane_v: in EmitCommonNeonBuiltinExpr()
6394 case NEON::BI__builtin_neon_vld3_lane_v: in EmitCommonNeonBuiltinExpr()
6395 case NEON::BI__builtin_neon_vld3q_lane_v: in EmitCommonNeonBuiltinExpr()
6396 case NEON::BI__builtin_neon_vld4_lane_v: in EmitCommonNeonBuiltinExpr()
6397 case NEON::BI__builtin_neon_vld4q_lane_v: { in EmitCommonNeonBuiltinExpr()
6408 case NEON::BI__builtin_neon_vmovl_v: { in EmitCommonNeonBuiltinExpr()
6416 case NEON::BI__builtin_neon_vmovn_v: { in EmitCommonNeonBuiltinExpr()
6422 case NEON::BI__builtin_neon_vmull_v: in EmitCommonNeonBuiltinExpr()
6431 case NEON::BI__builtin_neon_vpadal_v: in EmitCommonNeonBuiltinExpr()
6432 case NEON::BI__builtin_neon_vpadalq_v: { in EmitCommonNeonBuiltinExpr()
6442 case NEON::BI__builtin_neon_vpaddl_v: in EmitCommonNeonBuiltinExpr()
6443 case NEON::BI__builtin_neon_vpaddlq_v: { in EmitCommonNeonBuiltinExpr()
6452 case NEON::BI__builtin_neon_vqdmlal_v: in EmitCommonNeonBuiltinExpr()
6453 case NEON::BI__builtin_neon_vqdmlsl_v: { in EmitCommonNeonBuiltinExpr()
6460 case NEON::BI__builtin_neon_vqdmulhq_lane_v: in EmitCommonNeonBuiltinExpr()
6461 case NEON::BI__builtin_neon_vqdmulh_lane_v: in EmitCommonNeonBuiltinExpr()
6462 case NEON::BI__builtin_neon_vqrdmulhq_lane_v: in EmitCommonNeonBuiltinExpr()
6463 case NEON::BI__builtin_neon_vqrdmulh_lane_v: { in EmitCommonNeonBuiltinExpr()
6465 if (BuiltinID == NEON::BI__builtin_neon_vqdmulhq_lane_v || in EmitCommonNeonBuiltinExpr()
6466 BuiltinID == NEON::BI__builtin_neon_vqrdmulhq_lane_v) in EmitCommonNeonBuiltinExpr()
6474 case NEON::BI__builtin_neon_vqdmulhq_laneq_v: in EmitCommonNeonBuiltinExpr()
6475 case NEON::BI__builtin_neon_vqdmulh_laneq_v: in EmitCommonNeonBuiltinExpr()
6476 case NEON::BI__builtin_neon_vqrdmulhq_laneq_v: in EmitCommonNeonBuiltinExpr()
6477 case NEON::BI__builtin_neon_vqrdmulh_laneq_v: { in EmitCommonNeonBuiltinExpr()
6483 case NEON::BI__builtin_neon_vqshl_n_v: in EmitCommonNeonBuiltinExpr()
6484 case NEON::BI__builtin_neon_vqshlq_n_v: in EmitCommonNeonBuiltinExpr()
6487 case NEON::BI__builtin_neon_vqshlu_n_v: in EmitCommonNeonBuiltinExpr()
6488 case NEON::BI__builtin_neon_vqshluq_n_v: in EmitCommonNeonBuiltinExpr()
6491 case NEON::BI__builtin_neon_vrecpe_v: in EmitCommonNeonBuiltinExpr()
6492 case NEON::BI__builtin_neon_vrecpeq_v: in EmitCommonNeonBuiltinExpr()
6493 case NEON::BI__builtin_neon_vrsqrte_v: in EmitCommonNeonBuiltinExpr()
6494 case NEON::BI__builtin_neon_vrsqrteq_v: in EmitCommonNeonBuiltinExpr()
6497 case NEON::BI__builtin_neon_vrndi_v: in EmitCommonNeonBuiltinExpr()
6498 case NEON::BI__builtin_neon_vrndiq_v: in EmitCommonNeonBuiltinExpr()
6503 case NEON::BI__builtin_neon_vrshr_n_v: in EmitCommonNeonBuiltinExpr()
6504 case NEON::BI__builtin_neon_vrshrq_n_v: in EmitCommonNeonBuiltinExpr()
6507 case NEON::BI__builtin_neon_vshl_n_v: in EmitCommonNeonBuiltinExpr()
6508 case NEON::BI__builtin_neon_vshlq_n_v: in EmitCommonNeonBuiltinExpr()
6512 case NEON::BI__builtin_neon_vshll_n_v: { in EmitCommonNeonBuiltinExpr()
6523 case NEON::BI__builtin_neon_vshrn_n_v: { in EmitCommonNeonBuiltinExpr()
6534 case NEON::BI__builtin_neon_vshr_n_v: in EmitCommonNeonBuiltinExpr()
6535 case NEON::BI__builtin_neon_vshrq_n_v: in EmitCommonNeonBuiltinExpr()
6537 case NEON::BI__builtin_neon_vst1_v: in EmitCommonNeonBuiltinExpr()
6538 case NEON::BI__builtin_neon_vst1q_v: in EmitCommonNeonBuiltinExpr()
6539 case NEON::BI__builtin_neon_vst2_v: in EmitCommonNeonBuiltinExpr()
6540 case NEON::BI__builtin_neon_vst2q_v: in EmitCommonNeonBuiltinExpr()
6541 case NEON::BI__builtin_neon_vst3_v: in EmitCommonNeonBuiltinExpr()
6542 case NEON::BI__builtin_neon_vst3q_v: in EmitCommonNeonBuiltinExpr()
6543 case NEON::BI__builtin_neon_vst4_v: in EmitCommonNeonBuiltinExpr()
6544 case NEON::BI__builtin_neon_vst4q_v: in EmitCommonNeonBuiltinExpr()
6545 case NEON::BI__builtin_neon_vst2_lane_v: in EmitCommonNeonBuiltinExpr()
6546 case NEON::BI__builtin_neon_vst2q_lane_v: in EmitCommonNeonBuiltinExpr()
6547 case NEON::BI__builtin_neon_vst3_lane_v: in EmitCommonNeonBuiltinExpr()
6548 case NEON::BI__builtin_neon_vst3q_lane_v: in EmitCommonNeonBuiltinExpr()
6549 case NEON::BI__builtin_neon_vst4_lane_v: in EmitCommonNeonBuiltinExpr()
6550 case NEON::BI__builtin_neon_vst4q_lane_v: { in EmitCommonNeonBuiltinExpr()
6555 case NEON::BI__builtin_neon_vst1_x2_v: in EmitCommonNeonBuiltinExpr()
6556 case NEON::BI__builtin_neon_vst1q_x2_v: in EmitCommonNeonBuiltinExpr()
6557 case NEON::BI__builtin_neon_vst1_x3_v: in EmitCommonNeonBuiltinExpr()
6558 case NEON::BI__builtin_neon_vst1q_x3_v: in EmitCommonNeonBuiltinExpr()
6559 case NEON::BI__builtin_neon_vst1_x4_v: in EmitCommonNeonBuiltinExpr()
6560 case NEON::BI__builtin_neon_vst1q_x4_v: { in EmitCommonNeonBuiltinExpr()
6573 case NEON::BI__builtin_neon_vsubhn_v: { in EmitCommonNeonBuiltinExpr()
6590 case NEON::BI__builtin_neon_vtrn_v: in EmitCommonNeonBuiltinExpr()
6591 case NEON::BI__builtin_neon_vtrnq_v: { in EmitCommonNeonBuiltinExpr()
6609 case NEON::BI__builtin_neon_vtst_v: in EmitCommonNeonBuiltinExpr()
6610 case NEON::BI__builtin_neon_vtstq_v: { in EmitCommonNeonBuiltinExpr()
6618 case NEON::BI__builtin_neon_vuzp_v: in EmitCommonNeonBuiltinExpr()
6619 case NEON::BI__builtin_neon_vuzpq_v: { in EmitCommonNeonBuiltinExpr()
6636 case NEON::BI__builtin_neon_vzip_v: in EmitCommonNeonBuiltinExpr()
6637 case NEON::BI__builtin_neon_vzipq_v: { in EmitCommonNeonBuiltinExpr()
6655 case NEON::BI__builtin_neon_vdot_v: in EmitCommonNeonBuiltinExpr()
6656 case NEON::BI__builtin_neon_vdotq_v: { in EmitCommonNeonBuiltinExpr()
6663 case NEON::BI__builtin_neon_vfmlal_low_v: in EmitCommonNeonBuiltinExpr()
6664 case NEON::BI__builtin_neon_vfmlalq_low_v: { in EmitCommonNeonBuiltinExpr()
6670 case NEON::BI__builtin_neon_vfmlsl_low_v: in EmitCommonNeonBuiltinExpr()
6671 case NEON::BI__builtin_neon_vfmlslq_low_v: { in EmitCommonNeonBuiltinExpr()
6677 case NEON::BI__builtin_neon_vfmlal_high_v: in EmitCommonNeonBuiltinExpr()
6678 case NEON::BI__builtin_neon_vfmlalq_high_v: { in EmitCommonNeonBuiltinExpr()
6684 case NEON::BI__builtin_neon_vfmlsl_high_v: in EmitCommonNeonBuiltinExpr()
6685 case NEON::BI__builtin_neon_vfmlslq_high_v: { in EmitCommonNeonBuiltinExpr()
6691 case NEON::BI__builtin_neon_vmmlaq_v: { in EmitCommonNeonBuiltinExpr()
6698 case NEON::BI__builtin_neon_vusmmlaq_v: { in EmitCommonNeonBuiltinExpr()
6704 case NEON::BI__builtin_neon_vusdot_v: in EmitCommonNeonBuiltinExpr()
6705 case NEON::BI__builtin_neon_vusdotq_v: { in EmitCommonNeonBuiltinExpr()
6711 case NEON::BI__builtin_neon_vbfdot_v: in EmitCommonNeonBuiltinExpr()
6712 case NEON::BI__builtin_neon_vbfdotq_v: { in EmitCommonNeonBuiltinExpr()
6718 case NEON::BI__builtin_neon___a32_vcvt_bf16_v: { in EmitCommonNeonBuiltinExpr()
6911 case NEON::BI__builtin_neon_vget_lane_i8: in HasExtraNeonArgument()
6912 case NEON::BI__builtin_neon_vget_lane_i16: in HasExtraNeonArgument()
6913 case NEON::BI__builtin_neon_vget_lane_bf16: in HasExtraNeonArgument()
6914 case NEON::BI__builtin_neon_vget_lane_i32: in HasExtraNeonArgument()
6915 case NEON::BI__builtin_neon_vget_lane_i64: in HasExtraNeonArgument()
6916 case NEON::BI__builtin_neon_vget_lane_f32: in HasExtraNeonArgument()
6917 case NEON::BI__builtin_neon_vgetq_lane_i8: in HasExtraNeonArgument()
6918 case NEON::BI__builtin_neon_vgetq_lane_i16: in HasExtraNeonArgument()
6919 case NEON::BI__builtin_neon_vgetq_lane_bf16: in HasExtraNeonArgument()
6920 case NEON::BI__builtin_neon_vgetq_lane_i32: in HasExtraNeonArgument()
6921 case NEON::BI__builtin_neon_vgetq_lane_i64: in HasExtraNeonArgument()
6922 case NEON::BI__builtin_neon_vgetq_lane_f32: in HasExtraNeonArgument()
6923 case NEON::BI__builtin_neon_vduph_lane_bf16: in HasExtraNeonArgument()
6924 case NEON::BI__builtin_neon_vduph_laneq_bf16: in HasExtraNeonArgument()
6925 case NEON::BI__builtin_neon_vset_lane_i8: in HasExtraNeonArgument()
6926 case NEON::BI__builtin_neon_vset_lane_i16: in HasExtraNeonArgument()
6927 case NEON::BI__builtin_neon_vset_lane_bf16: in HasExtraNeonArgument()
6928 case NEON::BI__builtin_neon_vset_lane_i32: in HasExtraNeonArgument()
6929 case NEON::BI__builtin_neon_vset_lane_i64: in HasExtraNeonArgument()
6930 case NEON::BI__builtin_neon_vset_lane_f32: in HasExtraNeonArgument()
6931 case NEON::BI__builtin_neon_vsetq_lane_i8: in HasExtraNeonArgument()
6932 case NEON::BI__builtin_neon_vsetq_lane_i16: in HasExtraNeonArgument()
6933 case NEON::BI__builtin_neon_vsetq_lane_bf16: in HasExtraNeonArgument()
6934 case NEON::BI__builtin_neon_vsetq_lane_i32: in HasExtraNeonArgument()
6935 case NEON::BI__builtin_neon_vsetq_lane_i64: in HasExtraNeonArgument()
6936 case NEON::BI__builtin_neon_vsetq_lane_f32: in HasExtraNeonArgument()
6937 case NEON::BI__builtin_neon_vsha1h_u32: in HasExtraNeonArgument()
6938 case NEON::BI__builtin_neon_vsha1cq_u32: in HasExtraNeonArgument()
6939 case NEON::BI__builtin_neon_vsha1pq_u32: in HasExtraNeonArgument()
6940 case NEON::BI__builtin_neon_vsha1mq_u32: in HasExtraNeonArgument()
6941 case NEON::BI__builtin_neon_vcvth_bf16_f32: in HasExtraNeonArgument()
7312 case NEON::BI__builtin_neon_vld1_v: in EmitARMBuiltinExpr()
7313 case NEON::BI__builtin_neon_vld1q_v: in EmitARMBuiltinExpr()
7314 case NEON::BI__builtin_neon_vld1q_lane_v: in EmitARMBuiltinExpr()
7315 case NEON::BI__builtin_neon_vld1_lane_v: in EmitARMBuiltinExpr()
7316 case NEON::BI__builtin_neon_vld1_dup_v: in EmitARMBuiltinExpr()
7317 case NEON::BI__builtin_neon_vld1q_dup_v: in EmitARMBuiltinExpr()
7318 case NEON::BI__builtin_neon_vst1_v: in EmitARMBuiltinExpr()
7319 case NEON::BI__builtin_neon_vst1q_v: in EmitARMBuiltinExpr()
7320 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitARMBuiltinExpr()
7321 case NEON::BI__builtin_neon_vst1_lane_v: in EmitARMBuiltinExpr()
7322 case NEON::BI__builtin_neon_vst2_v: in EmitARMBuiltinExpr()
7323 case NEON::BI__builtin_neon_vst2q_v: in EmitARMBuiltinExpr()
7324 case NEON::BI__builtin_neon_vst2_lane_v: in EmitARMBuiltinExpr()
7325 case NEON::BI__builtin_neon_vst2q_lane_v: in EmitARMBuiltinExpr()
7326 case NEON::BI__builtin_neon_vst3_v: in EmitARMBuiltinExpr()
7327 case NEON::BI__builtin_neon_vst3q_v: in EmitARMBuiltinExpr()
7328 case NEON::BI__builtin_neon_vst3_lane_v: in EmitARMBuiltinExpr()
7329 case NEON::BI__builtin_neon_vst3q_lane_v: in EmitARMBuiltinExpr()
7330 case NEON::BI__builtin_neon_vst4_v: in EmitARMBuiltinExpr()
7331 case NEON::BI__builtin_neon_vst4q_v: in EmitARMBuiltinExpr()
7332 case NEON::BI__builtin_neon_vst4_lane_v: in EmitARMBuiltinExpr()
7333 case NEON::BI__builtin_neon_vst4q_lane_v: in EmitARMBuiltinExpr()
7343 case NEON::BI__builtin_neon_vld2_v: in EmitARMBuiltinExpr()
7344 case NEON::BI__builtin_neon_vld2q_v: in EmitARMBuiltinExpr()
7345 case NEON::BI__builtin_neon_vld3_v: in EmitARMBuiltinExpr()
7346 case NEON::BI__builtin_neon_vld3q_v: in EmitARMBuiltinExpr()
7347 case NEON::BI__builtin_neon_vld4_v: in EmitARMBuiltinExpr()
7348 case NEON::BI__builtin_neon_vld4q_v: in EmitARMBuiltinExpr()
7349 case NEON::BI__builtin_neon_vld2_lane_v: in EmitARMBuiltinExpr()
7350 case NEON::BI__builtin_neon_vld2q_lane_v: in EmitARMBuiltinExpr()
7351 case NEON::BI__builtin_neon_vld3_lane_v: in EmitARMBuiltinExpr()
7352 case NEON::BI__builtin_neon_vld3q_lane_v: in EmitARMBuiltinExpr()
7353 case NEON::BI__builtin_neon_vld4_lane_v: in EmitARMBuiltinExpr()
7354 case NEON::BI__builtin_neon_vld4q_lane_v: in EmitARMBuiltinExpr()
7355 case NEON::BI__builtin_neon_vld2_dup_v: in EmitARMBuiltinExpr()
7356 case NEON::BI__builtin_neon_vld2q_dup_v: in EmitARMBuiltinExpr()
7357 case NEON::BI__builtin_neon_vld3_dup_v: in EmitARMBuiltinExpr()
7358 case NEON::BI__builtin_neon_vld3q_dup_v: in EmitARMBuiltinExpr()
7359 case NEON::BI__builtin_neon_vld4_dup_v: in EmitARMBuiltinExpr()
7360 case NEON::BI__builtin_neon_vld4q_dup_v: in EmitARMBuiltinExpr()
7383 case NEON::BI__builtin_neon_vget_lane_i8: in EmitARMBuiltinExpr()
7384 case NEON::BI__builtin_neon_vget_lane_i16: in EmitARMBuiltinExpr()
7385 case NEON::BI__builtin_neon_vget_lane_i32: in EmitARMBuiltinExpr()
7386 case NEON::BI__builtin_neon_vget_lane_i64: in EmitARMBuiltinExpr()
7387 case NEON::BI__builtin_neon_vget_lane_bf16: in EmitARMBuiltinExpr()
7388 case NEON::BI__builtin_neon_vget_lane_f32: in EmitARMBuiltinExpr()
7389 case NEON::BI__builtin_neon_vgetq_lane_i8: in EmitARMBuiltinExpr()
7390 case NEON::BI__builtin_neon_vgetq_lane_i16: in EmitARMBuiltinExpr()
7391 case NEON::BI__builtin_neon_vgetq_lane_i32: in EmitARMBuiltinExpr()
7392 case NEON::BI__builtin_neon_vgetq_lane_i64: in EmitARMBuiltinExpr()
7393 case NEON::BI__builtin_neon_vgetq_lane_bf16: in EmitARMBuiltinExpr()
7394 case NEON::BI__builtin_neon_vgetq_lane_f32: in EmitARMBuiltinExpr()
7395 case NEON::BI__builtin_neon_vduph_lane_bf16: in EmitARMBuiltinExpr()
7396 case NEON::BI__builtin_neon_vduph_laneq_bf16: in EmitARMBuiltinExpr()
7399 case NEON::BI__builtin_neon_vrndns_f32: { in EmitARMBuiltinExpr()
7405 case NEON::BI__builtin_neon_vset_lane_i8: in EmitARMBuiltinExpr()
7406 case NEON::BI__builtin_neon_vset_lane_i16: in EmitARMBuiltinExpr()
7407 case NEON::BI__builtin_neon_vset_lane_i32: in EmitARMBuiltinExpr()
7408 case NEON::BI__builtin_neon_vset_lane_i64: in EmitARMBuiltinExpr()
7409 case NEON::BI__builtin_neon_vset_lane_bf16: in EmitARMBuiltinExpr()
7410 case NEON::BI__builtin_neon_vset_lane_f32: in EmitARMBuiltinExpr()
7411 case NEON::BI__builtin_neon_vsetq_lane_i8: in EmitARMBuiltinExpr()
7412 case NEON::BI__builtin_neon_vsetq_lane_i16: in EmitARMBuiltinExpr()
7413 case NEON::BI__builtin_neon_vsetq_lane_i32: in EmitARMBuiltinExpr()
7414 case NEON::BI__builtin_neon_vsetq_lane_i64: in EmitARMBuiltinExpr()
7415 case NEON::BI__builtin_neon_vsetq_lane_bf16: in EmitARMBuiltinExpr()
7416 case NEON::BI__builtin_neon_vsetq_lane_f32: in EmitARMBuiltinExpr()
7419 case NEON::BI__builtin_neon_vsha1h_u32: in EmitARMBuiltinExpr()
7422 case NEON::BI__builtin_neon_vsha1cq_u32: in EmitARMBuiltinExpr()
7425 case NEON::BI__builtin_neon_vsha1pq_u32: in EmitARMBuiltinExpr()
7428 case NEON::BI__builtin_neon_vsha1mq_u32: in EmitARMBuiltinExpr()
7432 case NEON::BI__builtin_neon_vcvth_bf16_f32: { in EmitARMBuiltinExpr()
7498 case NEON::BI__builtin_neon_vld1q_lane_v: in EmitARMBuiltinExpr()
7518 case NEON::BI__builtin_neon_vld1_lane_v: { in EmitARMBuiltinExpr()
7524 case NEON::BI__builtin_neon_vqrshrn_n_v: in EmitARMBuiltinExpr()
7529 case NEON::BI__builtin_neon_vqrshrun_n_v: in EmitARMBuiltinExpr()
7532 case NEON::BI__builtin_neon_vqshrn_n_v: in EmitARMBuiltinExpr()
7536 case NEON::BI__builtin_neon_vqshrun_n_v: in EmitARMBuiltinExpr()
7539 case NEON::BI__builtin_neon_vrecpe_v: in EmitARMBuiltinExpr()
7540 case NEON::BI__builtin_neon_vrecpeq_v: in EmitARMBuiltinExpr()
7543 case NEON::BI__builtin_neon_vrshrn_n_v: in EmitARMBuiltinExpr()
7546 case NEON::BI__builtin_neon_vrsra_n_v: in EmitARMBuiltinExpr()
7547 case NEON::BI__builtin_neon_vrsraq_n_v: in EmitARMBuiltinExpr()
7554 case NEON::BI__builtin_neon_vsri_n_v: in EmitARMBuiltinExpr()
7555 case NEON::BI__builtin_neon_vsriq_n_v: in EmitARMBuiltinExpr()
7558 case NEON::BI__builtin_neon_vsli_n_v: in EmitARMBuiltinExpr()
7559 case NEON::BI__builtin_neon_vsliq_n_v: in EmitARMBuiltinExpr()
7563 case NEON::BI__builtin_neon_vsra_n_v: in EmitARMBuiltinExpr()
7564 case NEON::BI__builtin_neon_vsraq_n_v: in EmitARMBuiltinExpr()
7568 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitARMBuiltinExpr()
7581 case NEON::BI__builtin_neon_vst1_lane_v: { in EmitARMBuiltinExpr()
7588 case NEON::BI__builtin_neon_vtbl1_v: in EmitARMBuiltinExpr()
7591 case NEON::BI__builtin_neon_vtbl2_v: in EmitARMBuiltinExpr()
7594 case NEON::BI__builtin_neon_vtbl3_v: in EmitARMBuiltinExpr()
7597 case NEON::BI__builtin_neon_vtbl4_v: in EmitARMBuiltinExpr()
7600 case NEON::BI__builtin_neon_vtbx1_v: in EmitARMBuiltinExpr()
7603 case NEON::BI__builtin_neon_vtbx2_v: in EmitARMBuiltinExpr()
7606 case NEON::BI__builtin_neon_vtbx3_v: in EmitARMBuiltinExpr()
7609 case NEON::BI__builtin_neon_vtbx4_v: in EmitARMBuiltinExpr()
7859 case NEON::BI__builtin_neon_vtbl1_v: in EmitAArch64TblBuiltinExpr()
7860 case NEON::BI__builtin_neon_vqtbl1_v: in EmitAArch64TblBuiltinExpr()
7861 case NEON::BI__builtin_neon_vqtbl1q_v: in EmitAArch64TblBuiltinExpr()
7862 case NEON::BI__builtin_neon_vtbl2_v: in EmitAArch64TblBuiltinExpr()
7863 case NEON::BI__builtin_neon_vqtbl2_v: in EmitAArch64TblBuiltinExpr()
7864 case NEON::BI__builtin_neon_vqtbl2q_v: in EmitAArch64TblBuiltinExpr()
7865 case NEON::BI__builtin_neon_vtbl3_v: in EmitAArch64TblBuiltinExpr()
7866 case NEON::BI__builtin_neon_vqtbl3_v: in EmitAArch64TblBuiltinExpr()
7867 case NEON::BI__builtin_neon_vqtbl3q_v: in EmitAArch64TblBuiltinExpr()
7868 case NEON::BI__builtin_neon_vtbl4_v: in EmitAArch64TblBuiltinExpr()
7869 case NEON::BI__builtin_neon_vqtbl4_v: in EmitAArch64TblBuiltinExpr()
7870 case NEON::BI__builtin_neon_vqtbl4q_v: in EmitAArch64TblBuiltinExpr()
7872 case NEON::BI__builtin_neon_vtbx1_v: in EmitAArch64TblBuiltinExpr()
7873 case NEON::BI__builtin_neon_vqtbx1_v: in EmitAArch64TblBuiltinExpr()
7874 case NEON::BI__builtin_neon_vqtbx1q_v: in EmitAArch64TblBuiltinExpr()
7875 case NEON::BI__builtin_neon_vtbx2_v: in EmitAArch64TblBuiltinExpr()
7876 case NEON::BI__builtin_neon_vqtbx2_v: in EmitAArch64TblBuiltinExpr()
7877 case NEON::BI__builtin_neon_vqtbx2q_v: in EmitAArch64TblBuiltinExpr()
7878 case NEON::BI__builtin_neon_vtbx3_v: in EmitAArch64TblBuiltinExpr()
7879 case NEON::BI__builtin_neon_vqtbx3_v: in EmitAArch64TblBuiltinExpr()
7880 case NEON::BI__builtin_neon_vqtbx3q_v: in EmitAArch64TblBuiltinExpr()
7881 case NEON::BI__builtin_neon_vtbx4_v: in EmitAArch64TblBuiltinExpr()
7882 case NEON::BI__builtin_neon_vqtbx4_v: in EmitAArch64TblBuiltinExpr()
7883 case NEON::BI__builtin_neon_vqtbx4q_v: in EmitAArch64TblBuiltinExpr()
7906 case NEON::BI__builtin_neon_vtbl1_v: { in EmitAArch64TblBuiltinExpr()
7911 case NEON::BI__builtin_neon_vtbl2_v: { in EmitAArch64TblBuiltinExpr()
7916 case NEON::BI__builtin_neon_vtbl3_v: { in EmitAArch64TblBuiltinExpr()
7921 case NEON::BI__builtin_neon_vtbl4_v: { in EmitAArch64TblBuiltinExpr()
7926 case NEON::BI__builtin_neon_vtbx1_v: { in EmitAArch64TblBuiltinExpr()
7939 case NEON::BI__builtin_neon_vtbx2_v: { in EmitAArch64TblBuiltinExpr()
7944 case NEON::BI__builtin_neon_vtbx3_v: { in EmitAArch64TblBuiltinExpr()
7958 case NEON::BI__builtin_neon_vtbx4_v: { in EmitAArch64TblBuiltinExpr()
7963 case NEON::BI__builtin_neon_vqtbl1_v: in EmitAArch64TblBuiltinExpr()
7964 case NEON::BI__builtin_neon_vqtbl1q_v: in EmitAArch64TblBuiltinExpr()
7966 case NEON::BI__builtin_neon_vqtbl2_v: in EmitAArch64TblBuiltinExpr()
7967 case NEON::BI__builtin_neon_vqtbl2q_v: { in EmitAArch64TblBuiltinExpr()
7969 case NEON::BI__builtin_neon_vqtbl3_v: in EmitAArch64TblBuiltinExpr()
7970 case NEON::BI__builtin_neon_vqtbl3q_v: in EmitAArch64TblBuiltinExpr()
7972 case NEON::BI__builtin_neon_vqtbl4_v: in EmitAArch64TblBuiltinExpr()
7973 case NEON::BI__builtin_neon_vqtbl4q_v: in EmitAArch64TblBuiltinExpr()
7975 case NEON::BI__builtin_neon_vqtbx1_v: in EmitAArch64TblBuiltinExpr()
7976 case NEON::BI__builtin_neon_vqtbx1q_v: in EmitAArch64TblBuiltinExpr()
7978 case NEON::BI__builtin_neon_vqtbx2_v: in EmitAArch64TblBuiltinExpr()
7979 case NEON::BI__builtin_neon_vqtbx2q_v: in EmitAArch64TblBuiltinExpr()
7981 case NEON::BI__builtin_neon_vqtbx3_v: in EmitAArch64TblBuiltinExpr()
7982 case NEON::BI__builtin_neon_vqtbx3q_v: in EmitAArch64TblBuiltinExpr()
7984 case NEON::BI__builtin_neon_vqtbx4_v: in EmitAArch64TblBuiltinExpr()
7985 case NEON::BI__builtin_neon_vqtbx4q_v: in EmitAArch64TblBuiltinExpr()
9268 case NEON::BI__builtin_neon_vld1_v: in EmitAArch64BuiltinExpr()
9269 case NEON::BI__builtin_neon_vld1q_v: in EmitAArch64BuiltinExpr()
9270 case NEON::BI__builtin_neon_vld1_dup_v: in EmitAArch64BuiltinExpr()
9271 case NEON::BI__builtin_neon_vld1q_dup_v: in EmitAArch64BuiltinExpr()
9272 case NEON::BI__builtin_neon_vld1_lane_v: in EmitAArch64BuiltinExpr()
9273 case NEON::BI__builtin_neon_vld1q_lane_v: in EmitAArch64BuiltinExpr()
9274 case NEON::BI__builtin_neon_vst1_v: in EmitAArch64BuiltinExpr()
9275 case NEON::BI__builtin_neon_vst1q_v: in EmitAArch64BuiltinExpr()
9276 case NEON::BI__builtin_neon_vst1_lane_v: in EmitAArch64BuiltinExpr()
9277 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitAArch64BuiltinExpr()
9319 case NEON::BI__builtin_neon_vabsh_f16: in EmitAArch64BuiltinExpr()
9322 case NEON::BI__builtin_neon_vldrq_p128: { in EmitAArch64BuiltinExpr()
9329 case NEON::BI__builtin_neon_vstrq_p128: { in EmitAArch64BuiltinExpr()
9334 case NEON::BI__builtin_neon_vcvts_f32_u32: in EmitAArch64BuiltinExpr()
9335 case NEON::BI__builtin_neon_vcvtd_f64_u64: in EmitAArch64BuiltinExpr()
9338 case NEON::BI__builtin_neon_vcvts_f32_s32: in EmitAArch64BuiltinExpr()
9339 case NEON::BI__builtin_neon_vcvtd_f64_s64: { in EmitAArch64BuiltinExpr()
9349 case NEON::BI__builtin_neon_vcvth_f16_u16: in EmitAArch64BuiltinExpr()
9350 case NEON::BI__builtin_neon_vcvth_f16_u32: in EmitAArch64BuiltinExpr()
9351 case NEON::BI__builtin_neon_vcvth_f16_u64: in EmitAArch64BuiltinExpr()
9354 case NEON::BI__builtin_neon_vcvth_f16_s16: in EmitAArch64BuiltinExpr()
9355 case NEON::BI__builtin_neon_vcvth_f16_s32: in EmitAArch64BuiltinExpr()
9356 case NEON::BI__builtin_neon_vcvth_f16_s64: { in EmitAArch64BuiltinExpr()
9371 case NEON::BI__builtin_neon_vcvtah_u16_f16: in EmitAArch64BuiltinExpr()
9372 case NEON::BI__builtin_neon_vcvtmh_u16_f16: in EmitAArch64BuiltinExpr()
9373 case NEON::BI__builtin_neon_vcvtnh_u16_f16: in EmitAArch64BuiltinExpr()
9374 case NEON::BI__builtin_neon_vcvtph_u16_f16: in EmitAArch64BuiltinExpr()
9375 case NEON::BI__builtin_neon_vcvth_u16_f16: in EmitAArch64BuiltinExpr()
9376 case NEON::BI__builtin_neon_vcvtah_s16_f16: in EmitAArch64BuiltinExpr()
9377 case NEON::BI__builtin_neon_vcvtmh_s16_f16: in EmitAArch64BuiltinExpr()
9378 case NEON::BI__builtin_neon_vcvtnh_s16_f16: in EmitAArch64BuiltinExpr()
9379 case NEON::BI__builtin_neon_vcvtph_s16_f16: in EmitAArch64BuiltinExpr()
9380 case NEON::BI__builtin_neon_vcvth_s16_f16: { in EmitAArch64BuiltinExpr()
9388 case NEON::BI__builtin_neon_vcvtah_u16_f16: in EmitAArch64BuiltinExpr()
9390 case NEON::BI__builtin_neon_vcvtmh_u16_f16: in EmitAArch64BuiltinExpr()
9392 case NEON::BI__builtin_neon_vcvtnh_u16_f16: in EmitAArch64BuiltinExpr()
9394 case NEON::BI__builtin_neon_vcvtph_u16_f16: in EmitAArch64BuiltinExpr()
9396 case NEON::BI__builtin_neon_vcvth_u16_f16: in EmitAArch64BuiltinExpr()
9398 case NEON::BI__builtin_neon_vcvtah_s16_f16: in EmitAArch64BuiltinExpr()
9400 case NEON::BI__builtin_neon_vcvtmh_s16_f16: in EmitAArch64BuiltinExpr()
9402 case NEON::BI__builtin_neon_vcvtnh_s16_f16: in EmitAArch64BuiltinExpr()
9404 case NEON::BI__builtin_neon_vcvtph_s16_f16: in EmitAArch64BuiltinExpr()
9406 case NEON::BI__builtin_neon_vcvth_s16_f16: in EmitAArch64BuiltinExpr()
9412 case NEON::BI__builtin_neon_vcaleh_f16: in EmitAArch64BuiltinExpr()
9413 case NEON::BI__builtin_neon_vcalth_f16: in EmitAArch64BuiltinExpr()
9414 case NEON::BI__builtin_neon_vcageh_f16: in EmitAArch64BuiltinExpr()
9415 case NEON::BI__builtin_neon_vcagth_f16: { in EmitAArch64BuiltinExpr()
9423 case NEON::BI__builtin_neon_vcageh_f16: in EmitAArch64BuiltinExpr()
9425 case NEON::BI__builtin_neon_vcagth_f16: in EmitAArch64BuiltinExpr()
9427 case NEON::BI__builtin_neon_vcaleh_f16: in EmitAArch64BuiltinExpr()
9429 case NEON::BI__builtin_neon_vcalth_f16: in EmitAArch64BuiltinExpr()
9435 case NEON::BI__builtin_neon_vcvth_n_s16_f16: in EmitAArch64BuiltinExpr()
9436 case NEON::BI__builtin_neon_vcvth_n_u16_f16: { in EmitAArch64BuiltinExpr()
9444 case NEON::BI__builtin_neon_vcvth_n_s16_f16: in EmitAArch64BuiltinExpr()
9446 case NEON::BI__builtin_neon_vcvth_n_u16_f16: in EmitAArch64BuiltinExpr()
9452 case NEON::BI__builtin_neon_vcvth_n_f16_s16: in EmitAArch64BuiltinExpr()
9453 case NEON::BI__builtin_neon_vcvth_n_f16_u16: { in EmitAArch64BuiltinExpr()
9461 case NEON::BI__builtin_neon_vcvth_n_f16_s16: in EmitAArch64BuiltinExpr()
9465 case NEON::BI__builtin_neon_vcvth_n_f16_u16: in EmitAArch64BuiltinExpr()
9472 case NEON::BI__builtin_neon_vpaddd_s64: { in EmitAArch64BuiltinExpr()
9484 case NEON::BI__builtin_neon_vpaddd_f64: { in EmitAArch64BuiltinExpr()
9496 case NEON::BI__builtin_neon_vpadds_f32: { in EmitAArch64BuiltinExpr()
9508 case NEON::BI__builtin_neon_vceqzd_s64: in EmitAArch64BuiltinExpr()
9509 case NEON::BI__builtin_neon_vceqzd_f64: in EmitAArch64BuiltinExpr()
9510 case NEON::BI__builtin_neon_vceqzs_f32: in EmitAArch64BuiltinExpr()
9511 case NEON::BI__builtin_neon_vceqzh_f16: in EmitAArch64BuiltinExpr()
9516 case NEON::BI__builtin_neon_vcgezd_s64: in EmitAArch64BuiltinExpr()
9517 case NEON::BI__builtin_neon_vcgezd_f64: in EmitAArch64BuiltinExpr()
9518 case NEON::BI__builtin_neon_vcgezs_f32: in EmitAArch64BuiltinExpr()
9519 case NEON::BI__builtin_neon_vcgezh_f16: in EmitAArch64BuiltinExpr()
9524 case NEON::BI__builtin_neon_vclezd_s64: in EmitAArch64BuiltinExpr()
9525 case NEON::BI__builtin_neon_vclezd_f64: in EmitAArch64BuiltinExpr()
9526 case NEON::BI__builtin_neon_vclezs_f32: in EmitAArch64BuiltinExpr()
9527 case NEON::BI__builtin_neon_vclezh_f16: in EmitAArch64BuiltinExpr()
9532 case NEON::BI__builtin_neon_vcgtzd_s64: in EmitAArch64BuiltinExpr()
9533 case NEON::BI__builtin_neon_vcgtzd_f64: in EmitAArch64BuiltinExpr()
9534 case NEON::BI__builtin_neon_vcgtzs_f32: in EmitAArch64BuiltinExpr()
9535 case NEON::BI__builtin_neon_vcgtzh_f16: in EmitAArch64BuiltinExpr()
9540 case NEON::BI__builtin_neon_vcltzd_s64: in EmitAArch64BuiltinExpr()
9541 case NEON::BI__builtin_neon_vcltzd_f64: in EmitAArch64BuiltinExpr()
9542 case NEON::BI__builtin_neon_vcltzs_f32: in EmitAArch64BuiltinExpr()
9543 case NEON::BI__builtin_neon_vcltzh_f16: in EmitAArch64BuiltinExpr()
9549 case NEON::BI__builtin_neon_vceqzd_u64: { in EmitAArch64BuiltinExpr()
9556 case NEON::BI__builtin_neon_vceqd_f64: in EmitAArch64BuiltinExpr()
9557 case NEON::BI__builtin_neon_vcled_f64: in EmitAArch64BuiltinExpr()
9558 case NEON::BI__builtin_neon_vcltd_f64: in EmitAArch64BuiltinExpr()
9559 case NEON::BI__builtin_neon_vcged_f64: in EmitAArch64BuiltinExpr()
9560 case NEON::BI__builtin_neon_vcgtd_f64: { in EmitAArch64BuiltinExpr()
9564 case NEON::BI__builtin_neon_vceqd_f64: P = llvm::FCmpInst::FCMP_OEQ; break; in EmitAArch64BuiltinExpr()
9565 case NEON::BI__builtin_neon_vcled_f64: P = llvm::FCmpInst::FCMP_OLE; break; in EmitAArch64BuiltinExpr()
9566 case NEON::BI__builtin_neon_vcltd_f64: P = llvm::FCmpInst::FCMP_OLT; break; in EmitAArch64BuiltinExpr()
9567 case NEON::BI__builtin_neon_vcged_f64: P = llvm::FCmpInst::FCMP_OGE; break; in EmitAArch64BuiltinExpr()
9568 case NEON::BI__builtin_neon_vcgtd_f64: P = llvm::FCmpInst::FCMP_OGT; break; in EmitAArch64BuiltinExpr()
9576 case NEON::BI__builtin_neon_vceqs_f32: in EmitAArch64BuiltinExpr()
9577 case NEON::BI__builtin_neon_vcles_f32: in EmitAArch64BuiltinExpr()
9578 case NEON::BI__builtin_neon_vclts_f32: in EmitAArch64BuiltinExpr()
9579 case NEON::BI__builtin_neon_vcges_f32: in EmitAArch64BuiltinExpr()
9580 case NEON::BI__builtin_neon_vcgts_f32: { in EmitAArch64BuiltinExpr()
9584 case NEON::BI__builtin_neon_vceqs_f32: P = llvm::FCmpInst::FCMP_OEQ; break; in EmitAArch64BuiltinExpr()
9585 case NEON::BI__builtin_neon_vcles_f32: P = llvm::FCmpInst::FCMP_OLE; break; in EmitAArch64BuiltinExpr()
9586 case NEON::BI__builtin_neon_vclts_f32: P = llvm::FCmpInst::FCMP_OLT; break; in EmitAArch64BuiltinExpr()
9587 case NEON::BI__builtin_neon_vcges_f32: P = llvm::FCmpInst::FCMP_OGE; break; in EmitAArch64BuiltinExpr()
9588 case NEON::BI__builtin_neon_vcgts_f32: P = llvm::FCmpInst::FCMP_OGT; break; in EmitAArch64BuiltinExpr()
9596 case NEON::BI__builtin_neon_vceqh_f16: in EmitAArch64BuiltinExpr()
9597 case NEON::BI__builtin_neon_vcleh_f16: in EmitAArch64BuiltinExpr()
9598 case NEON::BI__builtin_neon_vclth_f16: in EmitAArch64BuiltinExpr()
9599 case NEON::BI__builtin_neon_vcgeh_f16: in EmitAArch64BuiltinExpr()
9600 case NEON::BI__builtin_neon_vcgth_f16: { in EmitAArch64BuiltinExpr()
9604 case NEON::BI__builtin_neon_vceqh_f16: P = llvm::FCmpInst::FCMP_OEQ; break; in EmitAArch64BuiltinExpr()
9605 case NEON::BI__builtin_neon_vcleh_f16: P = llvm::FCmpInst::FCMP_OLE; break; in EmitAArch64BuiltinExpr()
9606 case NEON::BI__builtin_neon_vclth_f16: P = llvm::FCmpInst::FCMP_OLT; break; in EmitAArch64BuiltinExpr()
9607 case NEON::BI__builtin_neon_vcgeh_f16: P = llvm::FCmpInst::FCMP_OGE; break; in EmitAArch64BuiltinExpr()
9608 case NEON::BI__builtin_neon_vcgth_f16: P = llvm::FCmpInst::FCMP_OGT; break; in EmitAArch64BuiltinExpr()
9616 case NEON::BI__builtin_neon_vceqd_s64: in EmitAArch64BuiltinExpr()
9617 case NEON::BI__builtin_neon_vceqd_u64: in EmitAArch64BuiltinExpr()
9618 case NEON::BI__builtin_neon_vcgtd_s64: in EmitAArch64BuiltinExpr()
9619 case NEON::BI__builtin_neon_vcgtd_u64: in EmitAArch64BuiltinExpr()
9620 case NEON::BI__builtin_neon_vcltd_s64: in EmitAArch64BuiltinExpr()
9621 case NEON::BI__builtin_neon_vcltd_u64: in EmitAArch64BuiltinExpr()
9622 case NEON::BI__builtin_neon_vcged_u64: in EmitAArch64BuiltinExpr()
9623 case NEON::BI__builtin_neon_vcged_s64: in EmitAArch64BuiltinExpr()
9624 case NEON::BI__builtin_neon_vcled_u64: in EmitAArch64BuiltinExpr()
9625 case NEON::BI__builtin_neon_vcled_s64: { in EmitAArch64BuiltinExpr()
9629 case NEON::BI__builtin_neon_vceqd_s64: in EmitAArch64BuiltinExpr()
9630 case NEON::BI__builtin_neon_vceqd_u64:P = llvm::ICmpInst::ICMP_EQ;break; in EmitAArch64BuiltinExpr()
9631 case NEON::BI__builtin_neon_vcgtd_s64:P = llvm::ICmpInst::ICMP_SGT;break; in EmitAArch64BuiltinExpr()
9632 case NEON::BI__builtin_neon_vcgtd_u64:P = llvm::ICmpInst::ICMP_UGT;break; in EmitAArch64BuiltinExpr()
9633 case NEON::BI__builtin_neon_vcltd_s64:P = llvm::ICmpInst::ICMP_SLT;break; in EmitAArch64BuiltinExpr()
9634 case NEON::BI__builtin_neon_vcltd_u64:P = llvm::ICmpInst::ICMP_ULT;break; in EmitAArch64BuiltinExpr()
9635 case NEON::BI__builtin_neon_vcged_u64:P = llvm::ICmpInst::ICMP_UGE;break; in EmitAArch64BuiltinExpr()
9636 case NEON::BI__builtin_neon_vcged_s64:P = llvm::ICmpInst::ICMP_SGE;break; in EmitAArch64BuiltinExpr()
9637 case NEON::BI__builtin_neon_vcled_u64:P = llvm::ICmpInst::ICMP_ULE;break; in EmitAArch64BuiltinExpr()
9638 case NEON::BI__builtin_neon_vcled_s64:P = llvm::ICmpInst::ICMP_SLE;break; in EmitAArch64BuiltinExpr()
9646 case NEON::BI__builtin_neon_vtstd_s64: in EmitAArch64BuiltinExpr()
9647 case NEON::BI__builtin_neon_vtstd_u64: { in EmitAArch64BuiltinExpr()
9656 case NEON::BI__builtin_neon_vset_lane_i8: in EmitAArch64BuiltinExpr()
9657 case NEON::BI__builtin_neon_vset_lane_i16: in EmitAArch64BuiltinExpr()
9658 case NEON::BI__builtin_neon_vset_lane_i32: in EmitAArch64BuiltinExpr()
9659 case NEON::BI__builtin_neon_vset_lane_i64: in EmitAArch64BuiltinExpr()
9660 case NEON::BI__builtin_neon_vset_lane_bf16: in EmitAArch64BuiltinExpr()
9661 case NEON::BI__builtin_neon_vset_lane_f32: in EmitAArch64BuiltinExpr()
9662 case NEON::BI__builtin_neon_vsetq_lane_i8: in EmitAArch64BuiltinExpr()
9663 case NEON::BI__builtin_neon_vsetq_lane_i16: in EmitAArch64BuiltinExpr()
9664 case NEON::BI__builtin_neon_vsetq_lane_i32: in EmitAArch64BuiltinExpr()
9665 case NEON::BI__builtin_neon_vsetq_lane_i64: in EmitAArch64BuiltinExpr()
9666 case NEON::BI__builtin_neon_vsetq_lane_bf16: in EmitAArch64BuiltinExpr()
9667 case NEON::BI__builtin_neon_vsetq_lane_f32: in EmitAArch64BuiltinExpr()
9670 case NEON::BI__builtin_neon_vset_lane_f64: in EmitAArch64BuiltinExpr()
9676 case NEON::BI__builtin_neon_vsetq_lane_f64: in EmitAArch64BuiltinExpr()
9683 case NEON::BI__builtin_neon_vget_lane_i8: in EmitAArch64BuiltinExpr()
9684 case NEON::BI__builtin_neon_vdupb_lane_i8: in EmitAArch64BuiltinExpr()
9689 case NEON::BI__builtin_neon_vgetq_lane_i8: in EmitAArch64BuiltinExpr()
9690 case NEON::BI__builtin_neon_vdupb_laneq_i8: in EmitAArch64BuiltinExpr()
9695 case NEON::BI__builtin_neon_vget_lane_i16: in EmitAArch64BuiltinExpr()
9696 case NEON::BI__builtin_neon_vduph_lane_i16: in EmitAArch64BuiltinExpr()
9701 case NEON::BI__builtin_neon_vgetq_lane_i16: in EmitAArch64BuiltinExpr()
9702 case NEON::BI__builtin_neon_vduph_laneq_i16: in EmitAArch64BuiltinExpr()
9707 case NEON::BI__builtin_neon_vget_lane_i32: in EmitAArch64BuiltinExpr()
9708 case NEON::BI__builtin_neon_vdups_lane_i32: in EmitAArch64BuiltinExpr()
9713 case NEON::BI__builtin_neon_vdups_lane_f32: in EmitAArch64BuiltinExpr()
9718 case NEON::BI__builtin_neon_vgetq_lane_i32: in EmitAArch64BuiltinExpr()
9719 case NEON::BI__builtin_neon_vdups_laneq_i32: in EmitAArch64BuiltinExpr()
9724 case NEON::BI__builtin_neon_vget_lane_i64: in EmitAArch64BuiltinExpr()
9725 case NEON::BI__builtin_neon_vdupd_lane_i64: in EmitAArch64BuiltinExpr()
9730 case NEON::BI__builtin_neon_vdupd_lane_f64: in EmitAArch64BuiltinExpr()
9735 case NEON::BI__builtin_neon_vgetq_lane_i64: in EmitAArch64BuiltinExpr()
9736 case NEON::BI__builtin_neon_vdupd_laneq_i64: in EmitAArch64BuiltinExpr()
9741 case NEON::BI__builtin_neon_vget_lane_f32: in EmitAArch64BuiltinExpr()
9746 case NEON::BI__builtin_neon_vget_lane_f64: in EmitAArch64BuiltinExpr()
9751 case NEON::BI__builtin_neon_vgetq_lane_f32: in EmitAArch64BuiltinExpr()
9752 case NEON::BI__builtin_neon_vdups_laneq_f32: in EmitAArch64BuiltinExpr()
9757 case NEON::BI__builtin_neon_vgetq_lane_f64: in EmitAArch64BuiltinExpr()
9758 case NEON::BI__builtin_neon_vdupd_laneq_f64: in EmitAArch64BuiltinExpr()
9763 case NEON::BI__builtin_neon_vaddh_f16: in EmitAArch64BuiltinExpr()
9766 case NEON::BI__builtin_neon_vsubh_f16: in EmitAArch64BuiltinExpr()
9769 case NEON::BI__builtin_neon_vmulh_f16: in EmitAArch64BuiltinExpr()
9772 case NEON::BI__builtin_neon_vdivh_f16: in EmitAArch64BuiltinExpr()
9775 case NEON::BI__builtin_neon_vfmah_f16: in EmitAArch64BuiltinExpr()
9780 case NEON::BI__builtin_neon_vfmsh_f16: { in EmitAArch64BuiltinExpr()
9790 case NEON::BI__builtin_neon_vaddd_s64: in EmitAArch64BuiltinExpr()
9791 case NEON::BI__builtin_neon_vaddd_u64: in EmitAArch64BuiltinExpr()
9793 case NEON::BI__builtin_neon_vsubd_s64: in EmitAArch64BuiltinExpr()
9794 case NEON::BI__builtin_neon_vsubd_u64: in EmitAArch64BuiltinExpr()
9796 case NEON::BI__builtin_neon_vqdmlalh_s16: in EmitAArch64BuiltinExpr()
9797 case NEON::BI__builtin_neon_vqdmlslh_s16: { in EmitAArch64BuiltinExpr()
9807 unsigned AccumInt = BuiltinID == NEON::BI__builtin_neon_vqdmlalh_s16 in EmitAArch64BuiltinExpr()
9812 case NEON::BI__builtin_neon_vqshlud_n_s64: { in EmitAArch64BuiltinExpr()
9818 case NEON::BI__builtin_neon_vqshld_n_u64: in EmitAArch64BuiltinExpr()
9819 case NEON::BI__builtin_neon_vqshld_n_s64: { in EmitAArch64BuiltinExpr()
9820 unsigned Int = BuiltinID == NEON::BI__builtin_neon_vqshld_n_u64 in EmitAArch64BuiltinExpr()
9827 case NEON::BI__builtin_neon_vrshrd_n_u64: in EmitAArch64BuiltinExpr()
9828 case NEON::BI__builtin_neon_vrshrd_n_s64: { in EmitAArch64BuiltinExpr()
9829 unsigned Int = BuiltinID == NEON::BI__builtin_neon_vrshrd_n_u64 in EmitAArch64BuiltinExpr()
9837 case NEON::BI__builtin_neon_vrsrad_n_u64: in EmitAArch64BuiltinExpr()
9838 case NEON::BI__builtin_neon_vrsrad_n_s64: { in EmitAArch64BuiltinExpr()
9839 unsigned Int = BuiltinID == NEON::BI__builtin_neon_vrsrad_n_u64 in EmitAArch64BuiltinExpr()
9848 case NEON::BI__builtin_neon_vshld_n_s64: in EmitAArch64BuiltinExpr()
9849 case NEON::BI__builtin_neon_vshld_n_u64: { in EmitAArch64BuiltinExpr()
9854 case NEON::BI__builtin_neon_vshrd_n_s64: { in EmitAArch64BuiltinExpr()
9861 case NEON::BI__builtin_neon_vshrd_n_u64: { in EmitAArch64BuiltinExpr()
9870 case NEON::BI__builtin_neon_vsrad_n_s64: { in EmitAArch64BuiltinExpr()
9878 case NEON::BI__builtin_neon_vsrad_n_u64: { in EmitAArch64BuiltinExpr()
9889 case NEON::BI__builtin_neon_vqdmlalh_lane_s16: in EmitAArch64BuiltinExpr()
9890 case NEON::BI__builtin_neon_vqdmlalh_laneq_s16: in EmitAArch64BuiltinExpr()
9891 case NEON::BI__builtin_neon_vqdmlslh_lane_s16: in EmitAArch64BuiltinExpr()
9892 case NEON::BI__builtin_neon_vqdmlslh_laneq_s16: { in EmitAArch64BuiltinExpr()
9905 unsigned AccInt = (BuiltinID == NEON::BI__builtin_neon_vqdmlalh_lane_s16 || in EmitAArch64BuiltinExpr()
9906 BuiltinID == NEON::BI__builtin_neon_vqdmlalh_laneq_s16) in EmitAArch64BuiltinExpr()
9911 case NEON::BI__builtin_neon_vqdmlals_s32: in EmitAArch64BuiltinExpr()
9912 case NEON::BI__builtin_neon_vqdmlsls_s32: { in EmitAArch64BuiltinExpr()
9920 unsigned AccumInt = BuiltinID == NEON::BI__builtin_neon_vqdmlals_s32 in EmitAArch64BuiltinExpr()
9925 case NEON::BI__builtin_neon_vqdmlals_lane_s32: in EmitAArch64BuiltinExpr()
9926 case NEON::BI__builtin_neon_vqdmlals_laneq_s32: in EmitAArch64BuiltinExpr()
9927 case NEON::BI__builtin_neon_vqdmlsls_lane_s32: in EmitAArch64BuiltinExpr()
9928 case NEON::BI__builtin_neon_vqdmlsls_laneq_s32: { in EmitAArch64BuiltinExpr()
9939 unsigned AccInt = (BuiltinID == NEON::BI__builtin_neon_vqdmlals_lane_s32 || in EmitAArch64BuiltinExpr()
9940 BuiltinID == NEON::BI__builtin_neon_vqdmlals_laneq_s32) in EmitAArch64BuiltinExpr()
9945 case NEON::BI__builtin_neon_vget_lane_bf16: in EmitAArch64BuiltinExpr()
9946 case NEON::BI__builtin_neon_vduph_lane_bf16: in EmitAArch64BuiltinExpr()
9947 case NEON::BI__builtin_neon_vduph_lane_f16: { in EmitAArch64BuiltinExpr()
9951 case NEON::BI__builtin_neon_vgetq_lane_bf16: in EmitAArch64BuiltinExpr()
9952 case NEON::BI__builtin_neon_vduph_laneq_bf16: in EmitAArch64BuiltinExpr()
9953 case NEON::BI__builtin_neon_vduph_laneq_f16: { in EmitAArch64BuiltinExpr()
9990 case NEON::BI__builtin_neon_vbsl_v: in EmitAArch64BuiltinExpr()
9991 case NEON::BI__builtin_neon_vbslq_v: { in EmitAArch64BuiltinExpr()
10002 case NEON::BI__builtin_neon_vfma_lane_v: in EmitAArch64BuiltinExpr()
10003 case NEON::BI__builtin_neon_vfmaq_lane_v: { // Only used for FP types in EmitAArch64BuiltinExpr()
10014 auto *SourceTy = BuiltinID == NEON::BI__builtin_neon_vfmaq_lane_v in EmitAArch64BuiltinExpr()
10028 case NEON::BI__builtin_neon_vfma_laneq_v: { in EmitAArch64BuiltinExpr()
10058 case NEON::BI__builtin_neon_vfmaq_laneq_v: { in EmitAArch64BuiltinExpr()
10068 case NEON::BI__builtin_neon_vfmah_lane_f16: in EmitAArch64BuiltinExpr()
10069 case NEON::BI__builtin_neon_vfmas_lane_f32: in EmitAArch64BuiltinExpr()
10070 case NEON::BI__builtin_neon_vfmah_laneq_f16: in EmitAArch64BuiltinExpr()
10071 case NEON::BI__builtin_neon_vfmas_laneq_f32: in EmitAArch64BuiltinExpr()
10072 case NEON::BI__builtin_neon_vfmad_lane_f64: in EmitAArch64BuiltinExpr()
10073 case NEON::BI__builtin_neon_vfmad_laneq_f64: { in EmitAArch64BuiltinExpr()
10081 case NEON::BI__builtin_neon_vmull_v: in EmitAArch64BuiltinExpr()
10086 case NEON::BI__builtin_neon_vmax_v: in EmitAArch64BuiltinExpr()
10087 case NEON::BI__builtin_neon_vmaxq_v: in EmitAArch64BuiltinExpr()
10092 case NEON::BI__builtin_neon_vmaxh_f16: { in EmitAArch64BuiltinExpr()
10097 case NEON::BI__builtin_neon_vmin_v: in EmitAArch64BuiltinExpr()
10098 case NEON::BI__builtin_neon_vminq_v: in EmitAArch64BuiltinExpr()
10103 case NEON::BI__builtin_neon_vminh_f16: { in EmitAArch64BuiltinExpr()
10108 case NEON::BI__builtin_neon_vabd_v: in EmitAArch64BuiltinExpr()
10109 case NEON::BI__builtin_neon_vabdq_v: in EmitAArch64BuiltinExpr()
10114 case NEON::BI__builtin_neon_vpadal_v: in EmitAArch64BuiltinExpr()
10115 case NEON::BI__builtin_neon_vpadalq_v: { in EmitAArch64BuiltinExpr()
10130 case NEON::BI__builtin_neon_vpmin_v: in EmitAArch64BuiltinExpr()
10131 case NEON::BI__builtin_neon_vpminq_v: in EmitAArch64BuiltinExpr()
10136 case NEON::BI__builtin_neon_vpmax_v: in EmitAArch64BuiltinExpr()
10137 case NEON::BI__builtin_neon_vpmaxq_v: in EmitAArch64BuiltinExpr()
10142 case NEON::BI__builtin_neon_vminnm_v: in EmitAArch64BuiltinExpr()
10143 case NEON::BI__builtin_neon_vminnmq_v: in EmitAArch64BuiltinExpr()
10146 case NEON::BI__builtin_neon_vminnmh_f16: in EmitAArch64BuiltinExpr()
10150 case NEON::BI__builtin_neon_vmaxnm_v: in EmitAArch64BuiltinExpr()
10151 case NEON::BI__builtin_neon_vmaxnmq_v: in EmitAArch64BuiltinExpr()
10154 case NEON::BI__builtin_neon_vmaxnmh_f16: in EmitAArch64BuiltinExpr()
10158 case NEON::BI__builtin_neon_vrecpss_f32: { in EmitAArch64BuiltinExpr()
10163 case NEON::BI__builtin_neon_vrecpsd_f64: in EmitAArch64BuiltinExpr()
10167 case NEON::BI__builtin_neon_vrecpsh_f16: in EmitAArch64BuiltinExpr()
10171 case NEON::BI__builtin_neon_vqshrun_n_v: in EmitAArch64BuiltinExpr()
10174 case NEON::BI__builtin_neon_vqrshrun_n_v: in EmitAArch64BuiltinExpr()
10177 case NEON::BI__builtin_neon_vqshrn_n_v: in EmitAArch64BuiltinExpr()
10180 case NEON::BI__builtin_neon_vrshrn_n_v: in EmitAArch64BuiltinExpr()
10183 case NEON::BI__builtin_neon_vqrshrn_n_v: in EmitAArch64BuiltinExpr()
10186 case NEON::BI__builtin_neon_vrndah_f16: { in EmitAArch64BuiltinExpr()
10193 case NEON::BI__builtin_neon_vrnda_v: in EmitAArch64BuiltinExpr()
10194 case NEON::BI__builtin_neon_vrndaq_v: { in EmitAArch64BuiltinExpr()
10200 case NEON::BI__builtin_neon_vrndih_f16: { in EmitAArch64BuiltinExpr()
10207 case NEON::BI__builtin_neon_vrndmh_f16: { in EmitAArch64BuiltinExpr()
10214 case NEON::BI__builtin_neon_vrndm_v: in EmitAArch64BuiltinExpr()
10215 case NEON::BI__builtin_neon_vrndmq_v: { in EmitAArch64BuiltinExpr()
10221 case NEON::BI__builtin_neon_vrndnh_f16: { in EmitAArch64BuiltinExpr()
10226 case NEON::BI__builtin_neon_vrndn_v: in EmitAArch64BuiltinExpr()
10227 case NEON::BI__builtin_neon_vrndnq_v: { in EmitAArch64BuiltinExpr()
10231 case NEON::BI__builtin_neon_vrndns_f32: { in EmitAArch64BuiltinExpr()
10236 case NEON::BI__builtin_neon_vrndph_f16: { in EmitAArch64BuiltinExpr()
10243 case NEON::BI__builtin_neon_vrndp_v: in EmitAArch64BuiltinExpr()
10244 case NEON::BI__builtin_neon_vrndpq_v: { in EmitAArch64BuiltinExpr()
10250 case NEON::BI__builtin_neon_vrndxh_f16: { in EmitAArch64BuiltinExpr()
10257 case NEON::BI__builtin_neon_vrndx_v: in EmitAArch64BuiltinExpr()
10258 case NEON::BI__builtin_neon_vrndxq_v: { in EmitAArch64BuiltinExpr()
10264 case NEON::BI__builtin_neon_vrndh_f16: { in EmitAArch64BuiltinExpr()
10271 case NEON::BI__builtin_neon_vrnd_v: in EmitAArch64BuiltinExpr()
10272 case NEON::BI__builtin_neon_vrndq_v: { in EmitAArch64BuiltinExpr()
10278 case NEON::BI__builtin_neon_vcvt_f64_v: in EmitAArch64BuiltinExpr()
10279 case NEON::BI__builtin_neon_vcvtq_f64_v: in EmitAArch64BuiltinExpr()
10284 case NEON::BI__builtin_neon_vcvt_f64_f32: { in EmitAArch64BuiltinExpr()
10292 case NEON::BI__builtin_neon_vcvt_f32_f64: { in EmitAArch64BuiltinExpr()
10300 case NEON::BI__builtin_neon_vcvt_s32_v: in EmitAArch64BuiltinExpr()
10301 case NEON::BI__builtin_neon_vcvt_u32_v: in EmitAArch64BuiltinExpr()
10302 case NEON::BI__builtin_neon_vcvt_s64_v: in EmitAArch64BuiltinExpr()
10303 case NEON::BI__builtin_neon_vcvt_u64_v: in EmitAArch64BuiltinExpr()
10304 case NEON::BI__builtin_neon_vcvt_s16_v: in EmitAArch64BuiltinExpr()
10305 case NEON::BI__builtin_neon_vcvt_u16_v: in EmitAArch64BuiltinExpr()
10306 case NEON::BI__builtin_neon_vcvtq_s32_v: in EmitAArch64BuiltinExpr()
10307 case NEON::BI__builtin_neon_vcvtq_u32_v: in EmitAArch64BuiltinExpr()
10308 case NEON::BI__builtin_neon_vcvtq_s64_v: in EmitAArch64BuiltinExpr()
10309 case NEON::BI__builtin_neon_vcvtq_u64_v: in EmitAArch64BuiltinExpr()
10310 case NEON::BI__builtin_neon_vcvtq_s16_v: in EmitAArch64BuiltinExpr()
10311 case NEON::BI__builtin_neon_vcvtq_u16_v: { in EmitAArch64BuiltinExpr()
10317 case NEON::BI__builtin_neon_vcvta_s16_v: in EmitAArch64BuiltinExpr()
10318 case NEON::BI__builtin_neon_vcvta_u16_v: in EmitAArch64BuiltinExpr()
10319 case NEON::BI__builtin_neon_vcvta_s32_v: in EmitAArch64BuiltinExpr()
10320 case NEON::BI__builtin_neon_vcvtaq_s16_v: in EmitAArch64BuiltinExpr()
10321 case NEON::BI__builtin_neon_vcvtaq_s32_v: in EmitAArch64BuiltinExpr()
10322 case NEON::BI__builtin_neon_vcvta_u32_v: in EmitAArch64BuiltinExpr()
10323 case NEON::BI__builtin_neon_vcvtaq_u16_v: in EmitAArch64BuiltinExpr()
10324 case NEON::BI__builtin_neon_vcvtaq_u32_v: in EmitAArch64BuiltinExpr()
10325 case NEON::BI__builtin_neon_vcvta_s64_v: in EmitAArch64BuiltinExpr()
10326 case NEON::BI__builtin_neon_vcvtaq_s64_v: in EmitAArch64BuiltinExpr()
10327 case NEON::BI__builtin_neon_vcvta_u64_v: in EmitAArch64BuiltinExpr()
10328 case NEON::BI__builtin_neon_vcvtaq_u64_v: { in EmitAArch64BuiltinExpr()
10333 case NEON::BI__builtin_neon_vcvtm_s16_v: in EmitAArch64BuiltinExpr()
10334 case NEON::BI__builtin_neon_vcvtm_s32_v: in EmitAArch64BuiltinExpr()
10335 case NEON::BI__builtin_neon_vcvtmq_s16_v: in EmitAArch64BuiltinExpr()
10336 case NEON::BI__builtin_neon_vcvtmq_s32_v: in EmitAArch64BuiltinExpr()
10337 case NEON::BI__builtin_neon_vcvtm_u16_v: in EmitAArch64BuiltinExpr()
10338 case NEON::BI__builtin_neon_vcvtm_u32_v: in EmitAArch64BuiltinExpr()
10339 case NEON::BI__builtin_neon_vcvtmq_u16_v: in EmitAArch64BuiltinExpr()
10340 case NEON::BI__builtin_neon_vcvtmq_u32_v: in EmitAArch64BuiltinExpr()
10341 case NEON::BI__builtin_neon_vcvtm_s64_v: in EmitAArch64BuiltinExpr()
10342 case NEON::BI__builtin_neon_vcvtmq_s64_v: in EmitAArch64BuiltinExpr()
10343 case NEON::BI__builtin_neon_vcvtm_u64_v: in EmitAArch64BuiltinExpr()
10344 case NEON::BI__builtin_neon_vcvtmq_u64_v: { in EmitAArch64BuiltinExpr()
10349 case NEON::BI__builtin_neon_vcvtn_s16_v: in EmitAArch64BuiltinExpr()
10350 case NEON::BI__builtin_neon_vcvtn_s32_v: in EmitAArch64BuiltinExpr()
10351 case NEON::BI__builtin_neon_vcvtnq_s16_v: in EmitAArch64BuiltinExpr()
10352 case NEON::BI__builtin_neon_vcvtnq_s32_v: in EmitAArch64BuiltinExpr()
10353 case NEON::BI__builtin_neon_vcvtn_u16_v: in EmitAArch64BuiltinExpr()
10354 case NEON::BI__builtin_neon_vcvtn_u32_v: in EmitAArch64BuiltinExpr()
10355 case NEON::BI__builtin_neon_vcvtnq_u16_v: in EmitAArch64BuiltinExpr()
10356 case NEON::BI__builtin_neon_vcvtnq_u32_v: in EmitAArch64BuiltinExpr()
10357 case NEON::BI__builtin_neon_vcvtn_s64_v: in EmitAArch64BuiltinExpr()
10358 case NEON::BI__builtin_neon_vcvtnq_s64_v: in EmitAArch64BuiltinExpr()
10359 case NEON::BI__builtin_neon_vcvtn_u64_v: in EmitAArch64BuiltinExpr()
10360 case NEON::BI__builtin_neon_vcvtnq_u64_v: { in EmitAArch64BuiltinExpr()
10365 case NEON::BI__builtin_neon_vcvtp_s16_v: in EmitAArch64BuiltinExpr()
10366 case NEON::BI__builtin_neon_vcvtp_s32_v: in EmitAArch64BuiltinExpr()
10367 case NEON::BI__builtin_neon_vcvtpq_s16_v: in EmitAArch64BuiltinExpr()
10368 case NEON::BI__builtin_neon_vcvtpq_s32_v: in EmitAArch64BuiltinExpr()
10369 case NEON::BI__builtin_neon_vcvtp_u16_v: in EmitAArch64BuiltinExpr()
10370 case NEON::BI__builtin_neon_vcvtp_u32_v: in EmitAArch64BuiltinExpr()
10371 case NEON::BI__builtin_neon_vcvtpq_u16_v: in EmitAArch64BuiltinExpr()
10372 case NEON::BI__builtin_neon_vcvtpq_u32_v: in EmitAArch64BuiltinExpr()
10373 case NEON::BI__builtin_neon_vcvtp_s64_v: in EmitAArch64BuiltinExpr()
10374 case NEON::BI__builtin_neon_vcvtpq_s64_v: in EmitAArch64BuiltinExpr()
10375 case NEON::BI__builtin_neon_vcvtp_u64_v: in EmitAArch64BuiltinExpr()
10376 case NEON::BI__builtin_neon_vcvtpq_u64_v: { in EmitAArch64BuiltinExpr()
10381 case NEON::BI__builtin_neon_vmulx_v: in EmitAArch64BuiltinExpr()
10382 case NEON::BI__builtin_neon_vmulxq_v: { in EmitAArch64BuiltinExpr()
10386 case NEON::BI__builtin_neon_vmulxh_lane_f16: in EmitAArch64BuiltinExpr()
10387 case NEON::BI__builtin_neon_vmulxh_laneq_f16: { in EmitAArch64BuiltinExpr()
10396 case NEON::BI__builtin_neon_vmul_lane_v: in EmitAArch64BuiltinExpr()
10397 case NEON::BI__builtin_neon_vmul_laneq_v: { in EmitAArch64BuiltinExpr()
10400 if (BuiltinID == NEON::BI__builtin_neon_vmul_laneq_v) in EmitAArch64BuiltinExpr()
10410 case NEON::BI__builtin_neon_vnegd_s64: in EmitAArch64BuiltinExpr()
10412 case NEON::BI__builtin_neon_vnegh_f16: in EmitAArch64BuiltinExpr()
10414 case NEON::BI__builtin_neon_vpmaxnm_v: in EmitAArch64BuiltinExpr()
10415 case NEON::BI__builtin_neon_vpmaxnmq_v: { in EmitAArch64BuiltinExpr()
10419 case NEON::BI__builtin_neon_vpminnm_v: in EmitAArch64BuiltinExpr()
10420 case NEON::BI__builtin_neon_vpminnmq_v: { in EmitAArch64BuiltinExpr()
10424 case NEON::BI__builtin_neon_vsqrth_f16: { in EmitAArch64BuiltinExpr()
10431 case NEON::BI__builtin_neon_vsqrt_v: in EmitAArch64BuiltinExpr()
10432 case NEON::BI__builtin_neon_vsqrtq_v: { in EmitAArch64BuiltinExpr()
10439 case NEON::BI__builtin_neon_vrbit_v: in EmitAArch64BuiltinExpr()
10440 case NEON::BI__builtin_neon_vrbitq_v: { in EmitAArch64BuiltinExpr()
10444 case NEON::BI__builtin_neon_vaddv_u8: in EmitAArch64BuiltinExpr()
10448 case NEON::BI__builtin_neon_vaddv_s8: { in EmitAArch64BuiltinExpr()
10457 case NEON::BI__builtin_neon_vaddv_u16: in EmitAArch64BuiltinExpr()
10460 case NEON::BI__builtin_neon_vaddv_s16: { in EmitAArch64BuiltinExpr()
10469 case NEON::BI__builtin_neon_vaddvq_u8: in EmitAArch64BuiltinExpr()
10472 case NEON::BI__builtin_neon_vaddvq_s8: { in EmitAArch64BuiltinExpr()
10481 case NEON::BI__builtin_neon_vaddvq_u16: in EmitAArch64BuiltinExpr()
10484 case NEON::BI__builtin_neon_vaddvq_s16: { in EmitAArch64BuiltinExpr()
10493 case NEON::BI__builtin_neon_vmaxv_u8: { in EmitAArch64BuiltinExpr()
10502 case NEON::BI__builtin_neon_vmaxv_u16: { in EmitAArch64BuiltinExpr()
10511 case NEON::BI__builtin_neon_vmaxvq_u8: { in EmitAArch64BuiltinExpr()
10520 case NEON::BI__builtin_neon_vmaxvq_u16: { in EmitAArch64BuiltinExpr()
10529 case NEON::BI__builtin_neon_vmaxv_s8: { in EmitAArch64BuiltinExpr()
10538 case NEON::BI__builtin_neon_vmaxv_s16: { in EmitAArch64BuiltinExpr()
10547 case NEON::BI__builtin_neon_vmaxvq_s8: { in EmitAArch64BuiltinExpr()
10556 case NEON::BI__builtin_neon_vmaxvq_s16: { in EmitAArch64BuiltinExpr()
10565 case NEON::BI__builtin_neon_vmaxv_f16: { in EmitAArch64BuiltinExpr()
10574 case NEON::BI__builtin_neon_vmaxvq_f16: { in EmitAArch64BuiltinExpr()
10583 case NEON::BI__builtin_neon_vminv_u8: { in EmitAArch64BuiltinExpr()
10592 case NEON::BI__builtin_neon_vminv_u16: { in EmitAArch64BuiltinExpr()
10601 case NEON::BI__builtin_neon_vminvq_u8: { in EmitAArch64BuiltinExpr()
10610 case NEON::BI__builtin_neon_vminvq_u16: { in EmitAArch64BuiltinExpr()
10619 case NEON::BI__builtin_neon_vminv_s8: { in EmitAArch64BuiltinExpr()
10628 case NEON::BI__builtin_neon_vminv_s16: { in EmitAArch64BuiltinExpr()
10637 case NEON::BI__builtin_neon_vminvq_s8: { in EmitAArch64BuiltinExpr()
10646 case NEON::BI__builtin_neon_vminvq_s16: { in EmitAArch64BuiltinExpr()
10655 case NEON::BI__builtin_neon_vminv_f16: { in EmitAArch64BuiltinExpr()
10664 case NEON::BI__builtin_neon_vminvq_f16: { in EmitAArch64BuiltinExpr()
10673 case NEON::BI__builtin_neon_vmaxnmv_f16: { in EmitAArch64BuiltinExpr()
10682 case NEON::BI__builtin_neon_vmaxnmvq_f16: { in EmitAArch64BuiltinExpr()
10691 case NEON::BI__builtin_neon_vminnmv_f16: { in EmitAArch64BuiltinExpr()
10700 case NEON::BI__builtin_neon_vminnmvq_f16: { in EmitAArch64BuiltinExpr()
10709 case NEON::BI__builtin_neon_vmul_n_f64: { in EmitAArch64BuiltinExpr()
10714 case NEON::BI__builtin_neon_vaddlv_u8: { in EmitAArch64BuiltinExpr()
10723 case NEON::BI__builtin_neon_vaddlv_u16: { in EmitAArch64BuiltinExpr()
10731 case NEON::BI__builtin_neon_vaddlvq_u8: { in EmitAArch64BuiltinExpr()
10740 case NEON::BI__builtin_neon_vaddlvq_u16: { in EmitAArch64BuiltinExpr()
10748 case NEON::BI__builtin_neon_vaddlv_s8: { in EmitAArch64BuiltinExpr()
10757 case NEON::BI__builtin_neon_vaddlv_s16: { in EmitAArch64BuiltinExpr()
10765 case NEON::BI__builtin_neon_vaddlvq_s8: { in EmitAArch64BuiltinExpr()
10774 case NEON::BI__builtin_neon_vaddlvq_s16: { in EmitAArch64BuiltinExpr()
10782 case NEON::BI__builtin_neon_vsri_n_v: in EmitAArch64BuiltinExpr()
10783 case NEON::BI__builtin_neon_vsriq_n_v: { in EmitAArch64BuiltinExpr()
10788 case NEON::BI__builtin_neon_vsli_n_v: in EmitAArch64BuiltinExpr()
10789 case NEON::BI__builtin_neon_vsliq_n_v: { in EmitAArch64BuiltinExpr()
10794 case NEON::BI__builtin_neon_vsra_n_v: in EmitAArch64BuiltinExpr()
10795 case NEON::BI__builtin_neon_vsraq_n_v: in EmitAArch64BuiltinExpr()
10799 case NEON::BI__builtin_neon_vrsra_n_v: in EmitAArch64BuiltinExpr()
10800 case NEON::BI__builtin_neon_vrsraq_n_v: { in EmitAArch64BuiltinExpr()
10810 case NEON::BI__builtin_neon_vld1_v: in EmitAArch64BuiltinExpr()
10811 case NEON::BI__builtin_neon_vld1q_v: { in EmitAArch64BuiltinExpr()
10815 case NEON::BI__builtin_neon_vst1_v: in EmitAArch64BuiltinExpr()
10816 case NEON::BI__builtin_neon_vst1q_v: in EmitAArch64BuiltinExpr()
10820 case NEON::BI__builtin_neon_vld1_lane_v: in EmitAArch64BuiltinExpr()
10821 case NEON::BI__builtin_neon_vld1q_lane_v: { in EmitAArch64BuiltinExpr()
10829 case NEON::BI__builtin_neon_vld1_dup_v: in EmitAArch64BuiltinExpr()
10830 case NEON::BI__builtin_neon_vld1q_dup_v: { in EmitAArch64BuiltinExpr()
10840 case NEON::BI__builtin_neon_vst1_lane_v: in EmitAArch64BuiltinExpr()
10841 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitAArch64BuiltinExpr()
10847 case NEON::BI__builtin_neon_vld2_v: in EmitAArch64BuiltinExpr()
10848 case NEON::BI__builtin_neon_vld2q_v: { in EmitAArch64BuiltinExpr()
10858 case NEON::BI__builtin_neon_vld3_v: in EmitAArch64BuiltinExpr()
10859 case NEON::BI__builtin_neon_vld3q_v: { in EmitAArch64BuiltinExpr()
10869 case NEON::BI__builtin_neon_vld4_v: in EmitAArch64BuiltinExpr()
10870 case NEON::BI__builtin_neon_vld4q_v: { in EmitAArch64BuiltinExpr()
10880 case NEON::BI__builtin_neon_vld2_dup_v: in EmitAArch64BuiltinExpr()
10881 case NEON::BI__builtin_neon_vld2q_dup_v: { in EmitAArch64BuiltinExpr()
10892 case NEON::BI__builtin_neon_vld3_dup_v: in EmitAArch64BuiltinExpr()
10893 case NEON::BI__builtin_neon_vld3q_dup_v: { in EmitAArch64BuiltinExpr()
10904 case NEON::BI__builtin_neon_vld4_dup_v: in EmitAArch64BuiltinExpr()
10905 case NEON::BI__builtin_neon_vld4q_dup_v: { in EmitAArch64BuiltinExpr()
10916 case NEON::BI__builtin_neon_vld2_lane_v: in EmitAArch64BuiltinExpr()
10917 case NEON::BI__builtin_neon_vld2q_lane_v: { in EmitAArch64BuiltinExpr()
10929 case NEON::BI__builtin_neon_vld3_lane_v: in EmitAArch64BuiltinExpr()
10930 case NEON::BI__builtin_neon_vld3q_lane_v: { in EmitAArch64BuiltinExpr()
10943 case NEON::BI__builtin_neon_vld4_lane_v: in EmitAArch64BuiltinExpr()
10944 case NEON::BI__builtin_neon_vld4q_lane_v: { in EmitAArch64BuiltinExpr()
10958 case NEON::BI__builtin_neon_vst2_v: in EmitAArch64BuiltinExpr()
10959 case NEON::BI__builtin_neon_vst2q_v: { in EmitAArch64BuiltinExpr()
10965 case NEON::BI__builtin_neon_vst2_lane_v: in EmitAArch64BuiltinExpr()
10966 case NEON::BI__builtin_neon_vst2q_lane_v: { in EmitAArch64BuiltinExpr()
10973 case NEON::BI__builtin_neon_vst3_v: in EmitAArch64BuiltinExpr()
10974 case NEON::BI__builtin_neon_vst3q_v: { in EmitAArch64BuiltinExpr()
10980 case NEON::BI__builtin_neon_vst3_lane_v: in EmitAArch64BuiltinExpr()
10981 case NEON::BI__builtin_neon_vst3q_lane_v: { in EmitAArch64BuiltinExpr()
10988 case NEON::BI__builtin_neon_vst4_v: in EmitAArch64BuiltinExpr()
10989 case NEON::BI__builtin_neon_vst4q_v: { in EmitAArch64BuiltinExpr()
10995 case NEON::BI__builtin_neon_vst4_lane_v: in EmitAArch64BuiltinExpr()
10996 case NEON::BI__builtin_neon_vst4q_lane_v: { in EmitAArch64BuiltinExpr()
11003 case NEON::BI__builtin_neon_vtrn_v: in EmitAArch64BuiltinExpr()
11004 case NEON::BI__builtin_neon_vtrnq_v: { in EmitAArch64BuiltinExpr()
11022 case NEON::BI__builtin_neon_vuzp_v: in EmitAArch64BuiltinExpr()
11023 case NEON::BI__builtin_neon_vuzpq_v: { in EmitAArch64BuiltinExpr()
11040 case NEON::BI__builtin_neon_vzip_v: in EmitAArch64BuiltinExpr()
11041 case NEON::BI__builtin_neon_vzipq_v: { in EmitAArch64BuiltinExpr()
11059 case NEON::BI__builtin_neon_vqtbl1q_v: { in EmitAArch64BuiltinExpr()
11063 case NEON::BI__builtin_neon_vqtbl2q_v: { in EmitAArch64BuiltinExpr()
11067 case NEON::BI__builtin_neon_vqtbl3q_v: { in EmitAArch64BuiltinExpr()
11071 case NEON::BI__builtin_neon_vqtbl4q_v: { in EmitAArch64BuiltinExpr()
11075 case NEON::BI__builtin_neon_vqtbx1q_v: { in EmitAArch64BuiltinExpr()
11079 case NEON::BI__builtin_neon_vqtbx2q_v: { in EmitAArch64BuiltinExpr()
11083 case NEON::BI__builtin_neon_vqtbx3q_v: { in EmitAArch64BuiltinExpr()
11087 case NEON::BI__builtin_neon_vqtbx4q_v: { in EmitAArch64BuiltinExpr()
11091 case NEON::BI__builtin_neon_vsqadd_v: in EmitAArch64BuiltinExpr()
11092 case NEON::BI__builtin_neon_vsqaddq_v: { in EmitAArch64BuiltinExpr()
11096 case NEON::BI__builtin_neon_vuqadd_v: in EmitAArch64BuiltinExpr()
11097 case NEON::BI__builtin_neon_vuqaddq_v: { in EmitAArch64BuiltinExpr()