Lines Matching refs:NEON
2664 { #NameBase, NEON::BI__builtin_neon_ ## NameBase, 0, 0, 0 }
2667 { #NameBase, NEON:: BI__builtin_neon_ ## NameBase, \
2671 { #NameBase, NEON:: BI__builtin_neon_ ## NameBase, \
3281 case NEON::BI__builtin_neon_vcled_s64: in EmitCommonNeonSISDBuiltinExpr()
3282 case NEON::BI__builtin_neon_vcled_u64: in EmitCommonNeonSISDBuiltinExpr()
3283 case NEON::BI__builtin_neon_vcles_f32: in EmitCommonNeonSISDBuiltinExpr()
3284 case NEON::BI__builtin_neon_vcled_f64: in EmitCommonNeonSISDBuiltinExpr()
3285 case NEON::BI__builtin_neon_vcltd_s64: in EmitCommonNeonSISDBuiltinExpr()
3286 case NEON::BI__builtin_neon_vcltd_u64: in EmitCommonNeonSISDBuiltinExpr()
3287 case NEON::BI__builtin_neon_vclts_f32: in EmitCommonNeonSISDBuiltinExpr()
3288 case NEON::BI__builtin_neon_vcltd_f64: in EmitCommonNeonSISDBuiltinExpr()
3289 case NEON::BI__builtin_neon_vcales_f32: in EmitCommonNeonSISDBuiltinExpr()
3290 case NEON::BI__builtin_neon_vcaled_f64: in EmitCommonNeonSISDBuiltinExpr()
3291 case NEON::BI__builtin_neon_vcalts_f32: in EmitCommonNeonSISDBuiltinExpr()
3292 case NEON::BI__builtin_neon_vcaltd_f64: in EmitCommonNeonSISDBuiltinExpr()
3364 case NEON::BI__builtin_neon_vabs_v: in EmitCommonNeonBuiltinExpr()
3365 case NEON::BI__builtin_neon_vabsq_v: in EmitCommonNeonBuiltinExpr()
3369 case NEON::BI__builtin_neon_vaddhn_v: { in EmitCommonNeonBuiltinExpr()
3386 case NEON::BI__builtin_neon_vcale_v: in EmitCommonNeonBuiltinExpr()
3387 case NEON::BI__builtin_neon_vcaleq_v: in EmitCommonNeonBuiltinExpr()
3388 case NEON::BI__builtin_neon_vcalt_v: in EmitCommonNeonBuiltinExpr()
3389 case NEON::BI__builtin_neon_vcaltq_v: in EmitCommonNeonBuiltinExpr()
3391 case NEON::BI__builtin_neon_vcage_v: in EmitCommonNeonBuiltinExpr()
3392 case NEON::BI__builtin_neon_vcageq_v: in EmitCommonNeonBuiltinExpr()
3393 case NEON::BI__builtin_neon_vcagt_v: in EmitCommonNeonBuiltinExpr()
3394 case NEON::BI__builtin_neon_vcagtq_v: { in EmitCommonNeonBuiltinExpr()
3402 case NEON::BI__builtin_neon_vclz_v: in EmitCommonNeonBuiltinExpr()
3403 case NEON::BI__builtin_neon_vclzq_v: in EmitCommonNeonBuiltinExpr()
3408 case NEON::BI__builtin_neon_vcvt_f32_v: in EmitCommonNeonBuiltinExpr()
3409 case NEON::BI__builtin_neon_vcvtq_f32_v: in EmitCommonNeonBuiltinExpr()
3414 case NEON::BI__builtin_neon_vcvt_n_f32_v: in EmitCommonNeonBuiltinExpr()
3415 case NEON::BI__builtin_neon_vcvt_n_f64_v: in EmitCommonNeonBuiltinExpr()
3416 case NEON::BI__builtin_neon_vcvtq_n_f32_v: in EmitCommonNeonBuiltinExpr()
3417 case NEON::BI__builtin_neon_vcvtq_n_f64_v: { in EmitCommonNeonBuiltinExpr()
3423 case NEON::BI__builtin_neon_vcvt_n_s32_v: in EmitCommonNeonBuiltinExpr()
3424 case NEON::BI__builtin_neon_vcvt_n_u32_v: in EmitCommonNeonBuiltinExpr()
3425 case NEON::BI__builtin_neon_vcvt_n_s64_v: in EmitCommonNeonBuiltinExpr()
3426 case NEON::BI__builtin_neon_vcvt_n_u64_v: in EmitCommonNeonBuiltinExpr()
3427 case NEON::BI__builtin_neon_vcvtq_n_s32_v: in EmitCommonNeonBuiltinExpr()
3428 case NEON::BI__builtin_neon_vcvtq_n_u32_v: in EmitCommonNeonBuiltinExpr()
3429 case NEON::BI__builtin_neon_vcvtq_n_s64_v: in EmitCommonNeonBuiltinExpr()
3430 case NEON::BI__builtin_neon_vcvtq_n_u64_v: { in EmitCommonNeonBuiltinExpr()
3435 case NEON::BI__builtin_neon_vcvt_s32_v: in EmitCommonNeonBuiltinExpr()
3436 case NEON::BI__builtin_neon_vcvt_u32_v: in EmitCommonNeonBuiltinExpr()
3437 case NEON::BI__builtin_neon_vcvt_s64_v: in EmitCommonNeonBuiltinExpr()
3438 case NEON::BI__builtin_neon_vcvt_u64_v: in EmitCommonNeonBuiltinExpr()
3439 case NEON::BI__builtin_neon_vcvtq_s32_v: in EmitCommonNeonBuiltinExpr()
3440 case NEON::BI__builtin_neon_vcvtq_u32_v: in EmitCommonNeonBuiltinExpr()
3441 case NEON::BI__builtin_neon_vcvtq_s64_v: in EmitCommonNeonBuiltinExpr()
3442 case NEON::BI__builtin_neon_vcvtq_u64_v: { in EmitCommonNeonBuiltinExpr()
3447 case NEON::BI__builtin_neon_vcvta_s32_v: in EmitCommonNeonBuiltinExpr()
3448 case NEON::BI__builtin_neon_vcvta_s64_v: in EmitCommonNeonBuiltinExpr()
3449 case NEON::BI__builtin_neon_vcvta_u32_v: in EmitCommonNeonBuiltinExpr()
3450 case NEON::BI__builtin_neon_vcvta_u64_v: in EmitCommonNeonBuiltinExpr()
3451 case NEON::BI__builtin_neon_vcvtaq_s32_v: in EmitCommonNeonBuiltinExpr()
3452 case NEON::BI__builtin_neon_vcvtaq_s64_v: in EmitCommonNeonBuiltinExpr()
3453 case NEON::BI__builtin_neon_vcvtaq_u32_v: in EmitCommonNeonBuiltinExpr()
3454 case NEON::BI__builtin_neon_vcvtaq_u64_v: in EmitCommonNeonBuiltinExpr()
3455 case NEON::BI__builtin_neon_vcvtn_s32_v: in EmitCommonNeonBuiltinExpr()
3456 case NEON::BI__builtin_neon_vcvtn_s64_v: in EmitCommonNeonBuiltinExpr()
3457 case NEON::BI__builtin_neon_vcvtn_u32_v: in EmitCommonNeonBuiltinExpr()
3458 case NEON::BI__builtin_neon_vcvtn_u64_v: in EmitCommonNeonBuiltinExpr()
3459 case NEON::BI__builtin_neon_vcvtnq_s32_v: in EmitCommonNeonBuiltinExpr()
3460 case NEON::BI__builtin_neon_vcvtnq_s64_v: in EmitCommonNeonBuiltinExpr()
3461 case NEON::BI__builtin_neon_vcvtnq_u32_v: in EmitCommonNeonBuiltinExpr()
3462 case NEON::BI__builtin_neon_vcvtnq_u64_v: in EmitCommonNeonBuiltinExpr()
3463 case NEON::BI__builtin_neon_vcvtp_s32_v: in EmitCommonNeonBuiltinExpr()
3464 case NEON::BI__builtin_neon_vcvtp_s64_v: in EmitCommonNeonBuiltinExpr()
3465 case NEON::BI__builtin_neon_vcvtp_u32_v: in EmitCommonNeonBuiltinExpr()
3466 case NEON::BI__builtin_neon_vcvtp_u64_v: in EmitCommonNeonBuiltinExpr()
3467 case NEON::BI__builtin_neon_vcvtpq_s32_v: in EmitCommonNeonBuiltinExpr()
3468 case NEON::BI__builtin_neon_vcvtpq_s64_v: in EmitCommonNeonBuiltinExpr()
3469 case NEON::BI__builtin_neon_vcvtpq_u32_v: in EmitCommonNeonBuiltinExpr()
3470 case NEON::BI__builtin_neon_vcvtpq_u64_v: in EmitCommonNeonBuiltinExpr()
3471 case NEON::BI__builtin_neon_vcvtm_s32_v: in EmitCommonNeonBuiltinExpr()
3472 case NEON::BI__builtin_neon_vcvtm_s64_v: in EmitCommonNeonBuiltinExpr()
3473 case NEON::BI__builtin_neon_vcvtm_u32_v: in EmitCommonNeonBuiltinExpr()
3474 case NEON::BI__builtin_neon_vcvtm_u64_v: in EmitCommonNeonBuiltinExpr()
3475 case NEON::BI__builtin_neon_vcvtmq_s32_v: in EmitCommonNeonBuiltinExpr()
3476 case NEON::BI__builtin_neon_vcvtmq_s64_v: in EmitCommonNeonBuiltinExpr()
3477 case NEON::BI__builtin_neon_vcvtmq_u32_v: in EmitCommonNeonBuiltinExpr()
3478 case NEON::BI__builtin_neon_vcvtmq_u64_v: { in EmitCommonNeonBuiltinExpr()
3482 case NEON::BI__builtin_neon_vext_v: in EmitCommonNeonBuiltinExpr()
3483 case NEON::BI__builtin_neon_vextq_v: { in EmitCommonNeonBuiltinExpr()
3493 case NEON::BI__builtin_neon_vfma_v: in EmitCommonNeonBuiltinExpr()
3494 case NEON::BI__builtin_neon_vfmaq_v: { in EmitCommonNeonBuiltinExpr()
3503 case NEON::BI__builtin_neon_vld1_v: in EmitCommonNeonBuiltinExpr()
3504 case NEON::BI__builtin_neon_vld1q_v: { in EmitCommonNeonBuiltinExpr()
3509 case NEON::BI__builtin_neon_vld2_v: in EmitCommonNeonBuiltinExpr()
3510 case NEON::BI__builtin_neon_vld2q_v: in EmitCommonNeonBuiltinExpr()
3511 case NEON::BI__builtin_neon_vld3_v: in EmitCommonNeonBuiltinExpr()
3512 case NEON::BI__builtin_neon_vld3q_v: in EmitCommonNeonBuiltinExpr()
3513 case NEON::BI__builtin_neon_vld4_v: in EmitCommonNeonBuiltinExpr()
3514 case NEON::BI__builtin_neon_vld4q_v: { in EmitCommonNeonBuiltinExpr()
3523 case NEON::BI__builtin_neon_vld1_dup_v: in EmitCommonNeonBuiltinExpr()
3524 case NEON::BI__builtin_neon_vld1q_dup_v: { in EmitCommonNeonBuiltinExpr()
3533 case NEON::BI__builtin_neon_vld2_lane_v: in EmitCommonNeonBuiltinExpr()
3534 case NEON::BI__builtin_neon_vld2q_lane_v: in EmitCommonNeonBuiltinExpr()
3535 case NEON::BI__builtin_neon_vld3_lane_v: in EmitCommonNeonBuiltinExpr()
3536 case NEON::BI__builtin_neon_vld3q_lane_v: in EmitCommonNeonBuiltinExpr()
3537 case NEON::BI__builtin_neon_vld4_lane_v: in EmitCommonNeonBuiltinExpr()
3538 case NEON::BI__builtin_neon_vld4q_lane_v: { in EmitCommonNeonBuiltinExpr()
3549 case NEON::BI__builtin_neon_vmovl_v: { in EmitCommonNeonBuiltinExpr()
3556 case NEON::BI__builtin_neon_vmovn_v: { in EmitCommonNeonBuiltinExpr()
3561 case NEON::BI__builtin_neon_vmull_v: in EmitCommonNeonBuiltinExpr()
3570 case NEON::BI__builtin_neon_vpadal_v: in EmitCommonNeonBuiltinExpr()
3571 case NEON::BI__builtin_neon_vpadalq_v: { in EmitCommonNeonBuiltinExpr()
3581 case NEON::BI__builtin_neon_vpaddl_v: in EmitCommonNeonBuiltinExpr()
3582 case NEON::BI__builtin_neon_vpaddlq_v: { in EmitCommonNeonBuiltinExpr()
3591 case NEON::BI__builtin_neon_vqdmlal_v: in EmitCommonNeonBuiltinExpr()
3592 case NEON::BI__builtin_neon_vqdmlsl_v: { in EmitCommonNeonBuiltinExpr()
3599 case NEON::BI__builtin_neon_vqshl_n_v: in EmitCommonNeonBuiltinExpr()
3600 case NEON::BI__builtin_neon_vqshlq_n_v: in EmitCommonNeonBuiltinExpr()
3603 case NEON::BI__builtin_neon_vqshlu_n_v: in EmitCommonNeonBuiltinExpr()
3604 case NEON::BI__builtin_neon_vqshluq_n_v: in EmitCommonNeonBuiltinExpr()
3607 case NEON::BI__builtin_neon_vrecpe_v: in EmitCommonNeonBuiltinExpr()
3608 case NEON::BI__builtin_neon_vrecpeq_v: in EmitCommonNeonBuiltinExpr()
3609 case NEON::BI__builtin_neon_vrsqrte_v: in EmitCommonNeonBuiltinExpr()
3610 case NEON::BI__builtin_neon_vrsqrteq_v: in EmitCommonNeonBuiltinExpr()
3614 case NEON::BI__builtin_neon_vrshr_n_v: in EmitCommonNeonBuiltinExpr()
3615 case NEON::BI__builtin_neon_vrshrq_n_v: in EmitCommonNeonBuiltinExpr()
3618 case NEON::BI__builtin_neon_vshl_n_v: in EmitCommonNeonBuiltinExpr()
3619 case NEON::BI__builtin_neon_vshlq_n_v: in EmitCommonNeonBuiltinExpr()
3623 case NEON::BI__builtin_neon_vshll_n_v: { in EmitCommonNeonBuiltinExpr()
3633 case NEON::BI__builtin_neon_vshrn_n_v: { in EmitCommonNeonBuiltinExpr()
3643 case NEON::BI__builtin_neon_vshr_n_v: in EmitCommonNeonBuiltinExpr()
3644 case NEON::BI__builtin_neon_vshrq_n_v: in EmitCommonNeonBuiltinExpr()
3646 case NEON::BI__builtin_neon_vst1_v: in EmitCommonNeonBuiltinExpr()
3647 case NEON::BI__builtin_neon_vst1q_v: in EmitCommonNeonBuiltinExpr()
3648 case NEON::BI__builtin_neon_vst2_v: in EmitCommonNeonBuiltinExpr()
3649 case NEON::BI__builtin_neon_vst2q_v: in EmitCommonNeonBuiltinExpr()
3650 case NEON::BI__builtin_neon_vst3_v: in EmitCommonNeonBuiltinExpr()
3651 case NEON::BI__builtin_neon_vst3q_v: in EmitCommonNeonBuiltinExpr()
3652 case NEON::BI__builtin_neon_vst4_v: in EmitCommonNeonBuiltinExpr()
3653 case NEON::BI__builtin_neon_vst4q_v: in EmitCommonNeonBuiltinExpr()
3654 case NEON::BI__builtin_neon_vst2_lane_v: in EmitCommonNeonBuiltinExpr()
3655 case NEON::BI__builtin_neon_vst2q_lane_v: in EmitCommonNeonBuiltinExpr()
3656 case NEON::BI__builtin_neon_vst3_lane_v: in EmitCommonNeonBuiltinExpr()
3657 case NEON::BI__builtin_neon_vst3q_lane_v: in EmitCommonNeonBuiltinExpr()
3658 case NEON::BI__builtin_neon_vst4_lane_v: in EmitCommonNeonBuiltinExpr()
3659 case NEON::BI__builtin_neon_vst4q_lane_v: { in EmitCommonNeonBuiltinExpr()
3664 case NEON::BI__builtin_neon_vsubhn_v: { in EmitCommonNeonBuiltinExpr()
3681 case NEON::BI__builtin_neon_vtrn_v: in EmitCommonNeonBuiltinExpr()
3682 case NEON::BI__builtin_neon_vtrnq_v: { in EmitCommonNeonBuiltinExpr()
3700 case NEON::BI__builtin_neon_vtst_v: in EmitCommonNeonBuiltinExpr()
3701 case NEON::BI__builtin_neon_vtstq_v: { in EmitCommonNeonBuiltinExpr()
3709 case NEON::BI__builtin_neon_vuzp_v: in EmitCommonNeonBuiltinExpr()
3710 case NEON::BI__builtin_neon_vuzpq_v: { in EmitCommonNeonBuiltinExpr()
3727 case NEON::BI__builtin_neon_vzip_v: in EmitCommonNeonBuiltinExpr()
3728 case NEON::BI__builtin_neon_vzipq_v: { in EmitCommonNeonBuiltinExpr()
3923 case NEON::BI__builtin_neon_vget_lane_i8: in HasExtraNeonArgument()
3924 case NEON::BI__builtin_neon_vget_lane_i16: in HasExtraNeonArgument()
3925 case NEON::BI__builtin_neon_vget_lane_i32: in HasExtraNeonArgument()
3926 case NEON::BI__builtin_neon_vget_lane_i64: in HasExtraNeonArgument()
3927 case NEON::BI__builtin_neon_vget_lane_f32: in HasExtraNeonArgument()
3928 case NEON::BI__builtin_neon_vgetq_lane_i8: in HasExtraNeonArgument()
3929 case NEON::BI__builtin_neon_vgetq_lane_i16: in HasExtraNeonArgument()
3930 case NEON::BI__builtin_neon_vgetq_lane_i32: in HasExtraNeonArgument()
3931 case NEON::BI__builtin_neon_vgetq_lane_i64: in HasExtraNeonArgument()
3932 case NEON::BI__builtin_neon_vgetq_lane_f32: in HasExtraNeonArgument()
3933 case NEON::BI__builtin_neon_vset_lane_i8: in HasExtraNeonArgument()
3934 case NEON::BI__builtin_neon_vset_lane_i16: in HasExtraNeonArgument()
3935 case NEON::BI__builtin_neon_vset_lane_i32: in HasExtraNeonArgument()
3936 case NEON::BI__builtin_neon_vset_lane_i64: in HasExtraNeonArgument()
3937 case NEON::BI__builtin_neon_vset_lane_f32: in HasExtraNeonArgument()
3938 case NEON::BI__builtin_neon_vsetq_lane_i8: in HasExtraNeonArgument()
3939 case NEON::BI__builtin_neon_vsetq_lane_i16: in HasExtraNeonArgument()
3940 case NEON::BI__builtin_neon_vsetq_lane_i32: in HasExtraNeonArgument()
3941 case NEON::BI__builtin_neon_vsetq_lane_i64: in HasExtraNeonArgument()
3942 case NEON::BI__builtin_neon_vsetq_lane_f32: in HasExtraNeonArgument()
3943 case NEON::BI__builtin_neon_vsha1h_u32: in HasExtraNeonArgument()
3944 case NEON::BI__builtin_neon_vsha1cq_u32: in HasExtraNeonArgument()
3945 case NEON::BI__builtin_neon_vsha1pq_u32: in HasExtraNeonArgument()
3946 case NEON::BI__builtin_neon_vsha1mq_u32: in HasExtraNeonArgument()
4284 case NEON::BI__builtin_neon_vld1_v: in EmitARMBuiltinExpr()
4285 case NEON::BI__builtin_neon_vld1q_v: in EmitARMBuiltinExpr()
4286 case NEON::BI__builtin_neon_vld1q_lane_v: in EmitARMBuiltinExpr()
4287 case NEON::BI__builtin_neon_vld1_lane_v: in EmitARMBuiltinExpr()
4288 case NEON::BI__builtin_neon_vld1_dup_v: in EmitARMBuiltinExpr()
4289 case NEON::BI__builtin_neon_vld1q_dup_v: in EmitARMBuiltinExpr()
4290 case NEON::BI__builtin_neon_vst1_v: in EmitARMBuiltinExpr()
4291 case NEON::BI__builtin_neon_vst1q_v: in EmitARMBuiltinExpr()
4292 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitARMBuiltinExpr()
4293 case NEON::BI__builtin_neon_vst1_lane_v: in EmitARMBuiltinExpr()
4294 case NEON::BI__builtin_neon_vst2_v: in EmitARMBuiltinExpr()
4295 case NEON::BI__builtin_neon_vst2q_v: in EmitARMBuiltinExpr()
4296 case NEON::BI__builtin_neon_vst2_lane_v: in EmitARMBuiltinExpr()
4297 case NEON::BI__builtin_neon_vst2q_lane_v: in EmitARMBuiltinExpr()
4298 case NEON::BI__builtin_neon_vst3_v: in EmitARMBuiltinExpr()
4299 case NEON::BI__builtin_neon_vst3q_v: in EmitARMBuiltinExpr()
4300 case NEON::BI__builtin_neon_vst3_lane_v: in EmitARMBuiltinExpr()
4301 case NEON::BI__builtin_neon_vst3q_lane_v: in EmitARMBuiltinExpr()
4302 case NEON::BI__builtin_neon_vst4_v: in EmitARMBuiltinExpr()
4303 case NEON::BI__builtin_neon_vst4q_v: in EmitARMBuiltinExpr()
4304 case NEON::BI__builtin_neon_vst4_lane_v: in EmitARMBuiltinExpr()
4305 case NEON::BI__builtin_neon_vst4q_lane_v: in EmitARMBuiltinExpr()
4315 case NEON::BI__builtin_neon_vld2_v: in EmitARMBuiltinExpr()
4316 case NEON::BI__builtin_neon_vld2q_v: in EmitARMBuiltinExpr()
4317 case NEON::BI__builtin_neon_vld3_v: in EmitARMBuiltinExpr()
4318 case NEON::BI__builtin_neon_vld3q_v: in EmitARMBuiltinExpr()
4319 case NEON::BI__builtin_neon_vld4_v: in EmitARMBuiltinExpr()
4320 case NEON::BI__builtin_neon_vld4q_v: in EmitARMBuiltinExpr()
4321 case NEON::BI__builtin_neon_vld2_lane_v: in EmitARMBuiltinExpr()
4322 case NEON::BI__builtin_neon_vld2q_lane_v: in EmitARMBuiltinExpr()
4323 case NEON::BI__builtin_neon_vld3_lane_v: in EmitARMBuiltinExpr()
4324 case NEON::BI__builtin_neon_vld3q_lane_v: in EmitARMBuiltinExpr()
4325 case NEON::BI__builtin_neon_vld4_lane_v: in EmitARMBuiltinExpr()
4326 case NEON::BI__builtin_neon_vld4q_lane_v: in EmitARMBuiltinExpr()
4327 case NEON::BI__builtin_neon_vld2_dup_v: in EmitARMBuiltinExpr()
4328 case NEON::BI__builtin_neon_vld3_dup_v: in EmitARMBuiltinExpr()
4329 case NEON::BI__builtin_neon_vld4_dup_v: in EmitARMBuiltinExpr()
4353 case NEON::BI__builtin_neon_vget_lane_i8: in EmitARMBuiltinExpr()
4354 case NEON::BI__builtin_neon_vget_lane_i16: in EmitARMBuiltinExpr()
4355 case NEON::BI__builtin_neon_vget_lane_i32: in EmitARMBuiltinExpr()
4356 case NEON::BI__builtin_neon_vget_lane_i64: in EmitARMBuiltinExpr()
4357 case NEON::BI__builtin_neon_vget_lane_f32: in EmitARMBuiltinExpr()
4358 case NEON::BI__builtin_neon_vgetq_lane_i8: in EmitARMBuiltinExpr()
4359 case NEON::BI__builtin_neon_vgetq_lane_i16: in EmitARMBuiltinExpr()
4360 case NEON::BI__builtin_neon_vgetq_lane_i32: in EmitARMBuiltinExpr()
4361 case NEON::BI__builtin_neon_vgetq_lane_i64: in EmitARMBuiltinExpr()
4362 case NEON::BI__builtin_neon_vgetq_lane_f32: in EmitARMBuiltinExpr()
4365 case NEON::BI__builtin_neon_vset_lane_i8: in EmitARMBuiltinExpr()
4366 case NEON::BI__builtin_neon_vset_lane_i16: in EmitARMBuiltinExpr()
4367 case NEON::BI__builtin_neon_vset_lane_i32: in EmitARMBuiltinExpr()
4368 case NEON::BI__builtin_neon_vset_lane_i64: in EmitARMBuiltinExpr()
4369 case NEON::BI__builtin_neon_vset_lane_f32: in EmitARMBuiltinExpr()
4370 case NEON::BI__builtin_neon_vsetq_lane_i8: in EmitARMBuiltinExpr()
4371 case NEON::BI__builtin_neon_vsetq_lane_i16: in EmitARMBuiltinExpr()
4372 case NEON::BI__builtin_neon_vsetq_lane_i32: in EmitARMBuiltinExpr()
4373 case NEON::BI__builtin_neon_vsetq_lane_i64: in EmitARMBuiltinExpr()
4374 case NEON::BI__builtin_neon_vsetq_lane_f32: in EmitARMBuiltinExpr()
4377 case NEON::BI__builtin_neon_vsha1h_u32: in EmitARMBuiltinExpr()
4380 case NEON::BI__builtin_neon_vsha1cq_u32: in EmitARMBuiltinExpr()
4383 case NEON::BI__builtin_neon_vsha1pq_u32: in EmitARMBuiltinExpr()
4386 case NEON::BI__builtin_neon_vsha1mq_u32: in EmitARMBuiltinExpr()
4449 case NEON::BI__builtin_neon_vld1q_lane_v: in EmitARMBuiltinExpr()
4470 case NEON::BI__builtin_neon_vld1_lane_v: { in EmitARMBuiltinExpr()
4476 case NEON::BI__builtin_neon_vld2_dup_v: in EmitARMBuiltinExpr()
4477 case NEON::BI__builtin_neon_vld3_dup_v: in EmitARMBuiltinExpr()
4478 case NEON::BI__builtin_neon_vld4_dup_v: { in EmitARMBuiltinExpr()
4482 case NEON::BI__builtin_neon_vld2_dup_v: in EmitARMBuiltinExpr()
4485 case NEON::BI__builtin_neon_vld3_dup_v: in EmitARMBuiltinExpr()
4488 case NEON::BI__builtin_neon_vld4_dup_v: in EmitARMBuiltinExpr()
4502 case NEON::BI__builtin_neon_vld2_dup_v: in EmitARMBuiltinExpr()
4505 case NEON::BI__builtin_neon_vld3_dup_v: in EmitARMBuiltinExpr()
4508 case NEON::BI__builtin_neon_vld4_dup_v: in EmitARMBuiltinExpr()
4538 case NEON::BI__builtin_neon_vqrshrn_n_v: in EmitARMBuiltinExpr()
4543 case NEON::BI__builtin_neon_vqrshrun_n_v: in EmitARMBuiltinExpr()
4546 case NEON::BI__builtin_neon_vqshrn_n_v: in EmitARMBuiltinExpr()
4550 case NEON::BI__builtin_neon_vqshrun_n_v: in EmitARMBuiltinExpr()
4553 case NEON::BI__builtin_neon_vrecpe_v: in EmitARMBuiltinExpr()
4554 case NEON::BI__builtin_neon_vrecpeq_v: in EmitARMBuiltinExpr()
4557 case NEON::BI__builtin_neon_vrshrn_n_v: in EmitARMBuiltinExpr()
4560 case NEON::BI__builtin_neon_vrsra_n_v: in EmitARMBuiltinExpr()
4561 case NEON::BI__builtin_neon_vrsraq_n_v: in EmitARMBuiltinExpr()
4568 case NEON::BI__builtin_neon_vsri_n_v: in EmitARMBuiltinExpr()
4569 case NEON::BI__builtin_neon_vsriq_n_v: in EmitARMBuiltinExpr()
4571 case NEON::BI__builtin_neon_vsli_n_v: in EmitARMBuiltinExpr()
4572 case NEON::BI__builtin_neon_vsliq_n_v: in EmitARMBuiltinExpr()
4576 case NEON::BI__builtin_neon_vsra_n_v: in EmitARMBuiltinExpr()
4577 case NEON::BI__builtin_neon_vsraq_n_v: in EmitARMBuiltinExpr()
4581 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitARMBuiltinExpr()
4594 case NEON::BI__builtin_neon_vst1_lane_v: { in EmitARMBuiltinExpr()
4601 case NEON::BI__builtin_neon_vtbl1_v: in EmitARMBuiltinExpr()
4604 case NEON::BI__builtin_neon_vtbl2_v: in EmitARMBuiltinExpr()
4607 case NEON::BI__builtin_neon_vtbl3_v: in EmitARMBuiltinExpr()
4610 case NEON::BI__builtin_neon_vtbl4_v: in EmitARMBuiltinExpr()
4613 case NEON::BI__builtin_neon_vtbx1_v: in EmitARMBuiltinExpr()
4616 case NEON::BI__builtin_neon_vtbx2_v: in EmitARMBuiltinExpr()
4619 case NEON::BI__builtin_neon_vtbx3_v: in EmitARMBuiltinExpr()
4622 case NEON::BI__builtin_neon_vtbx4_v: in EmitARMBuiltinExpr()
4637 case NEON::BI__builtin_neon_vtbl1_v: in EmitAArch64TblBuiltinExpr()
4638 case NEON::BI__builtin_neon_vqtbl1_v: in EmitAArch64TblBuiltinExpr()
4639 case NEON::BI__builtin_neon_vqtbl1q_v: in EmitAArch64TblBuiltinExpr()
4640 case NEON::BI__builtin_neon_vtbl2_v: in EmitAArch64TblBuiltinExpr()
4641 case NEON::BI__builtin_neon_vqtbl2_v: in EmitAArch64TblBuiltinExpr()
4642 case NEON::BI__builtin_neon_vqtbl2q_v: in EmitAArch64TblBuiltinExpr()
4643 case NEON::BI__builtin_neon_vtbl3_v: in EmitAArch64TblBuiltinExpr()
4644 case NEON::BI__builtin_neon_vqtbl3_v: in EmitAArch64TblBuiltinExpr()
4645 case NEON::BI__builtin_neon_vqtbl3q_v: in EmitAArch64TblBuiltinExpr()
4646 case NEON::BI__builtin_neon_vtbl4_v: in EmitAArch64TblBuiltinExpr()
4647 case NEON::BI__builtin_neon_vqtbl4_v: in EmitAArch64TblBuiltinExpr()
4648 case NEON::BI__builtin_neon_vqtbl4q_v: in EmitAArch64TblBuiltinExpr()
4650 case NEON::BI__builtin_neon_vtbx1_v: in EmitAArch64TblBuiltinExpr()
4651 case NEON::BI__builtin_neon_vqtbx1_v: in EmitAArch64TblBuiltinExpr()
4652 case NEON::BI__builtin_neon_vqtbx1q_v: in EmitAArch64TblBuiltinExpr()
4653 case NEON::BI__builtin_neon_vtbx2_v: in EmitAArch64TblBuiltinExpr()
4654 case NEON::BI__builtin_neon_vqtbx2_v: in EmitAArch64TblBuiltinExpr()
4655 case NEON::BI__builtin_neon_vqtbx2q_v: in EmitAArch64TblBuiltinExpr()
4656 case NEON::BI__builtin_neon_vtbx3_v: in EmitAArch64TblBuiltinExpr()
4657 case NEON::BI__builtin_neon_vqtbx3_v: in EmitAArch64TblBuiltinExpr()
4658 case NEON::BI__builtin_neon_vqtbx3q_v: in EmitAArch64TblBuiltinExpr()
4659 case NEON::BI__builtin_neon_vtbx4_v: in EmitAArch64TblBuiltinExpr()
4660 case NEON::BI__builtin_neon_vqtbx4_v: in EmitAArch64TblBuiltinExpr()
4661 case NEON::BI__builtin_neon_vqtbx4q_v: in EmitAArch64TblBuiltinExpr()
4684 case NEON::BI__builtin_neon_vtbl1_v: { in EmitAArch64TblBuiltinExpr()
4689 case NEON::BI__builtin_neon_vtbl2_v: { in EmitAArch64TblBuiltinExpr()
4694 case NEON::BI__builtin_neon_vtbl3_v: { in EmitAArch64TblBuiltinExpr()
4699 case NEON::BI__builtin_neon_vtbl4_v: { in EmitAArch64TblBuiltinExpr()
4704 case NEON::BI__builtin_neon_vtbx1_v: { in EmitAArch64TblBuiltinExpr()
4717 case NEON::BI__builtin_neon_vtbx2_v: { in EmitAArch64TblBuiltinExpr()
4722 case NEON::BI__builtin_neon_vtbx3_v: { in EmitAArch64TblBuiltinExpr()
4736 case NEON::BI__builtin_neon_vtbx4_v: { in EmitAArch64TblBuiltinExpr()
4741 case NEON::BI__builtin_neon_vqtbl1_v: in EmitAArch64TblBuiltinExpr()
4742 case NEON::BI__builtin_neon_vqtbl1q_v: in EmitAArch64TblBuiltinExpr()
4744 case NEON::BI__builtin_neon_vqtbl2_v: in EmitAArch64TblBuiltinExpr()
4745 case NEON::BI__builtin_neon_vqtbl2q_v: { in EmitAArch64TblBuiltinExpr()
4747 case NEON::BI__builtin_neon_vqtbl3_v: in EmitAArch64TblBuiltinExpr()
4748 case NEON::BI__builtin_neon_vqtbl3q_v: in EmitAArch64TblBuiltinExpr()
4750 case NEON::BI__builtin_neon_vqtbl4_v: in EmitAArch64TblBuiltinExpr()
4751 case NEON::BI__builtin_neon_vqtbl4q_v: in EmitAArch64TblBuiltinExpr()
4753 case NEON::BI__builtin_neon_vqtbx1_v: in EmitAArch64TblBuiltinExpr()
4754 case NEON::BI__builtin_neon_vqtbx1q_v: in EmitAArch64TblBuiltinExpr()
4756 case NEON::BI__builtin_neon_vqtbx2_v: in EmitAArch64TblBuiltinExpr()
4757 case NEON::BI__builtin_neon_vqtbx2q_v: in EmitAArch64TblBuiltinExpr()
4759 case NEON::BI__builtin_neon_vqtbx3_v: in EmitAArch64TblBuiltinExpr()
4760 case NEON::BI__builtin_neon_vqtbx3q_v: in EmitAArch64TblBuiltinExpr()
4762 case NEON::BI__builtin_neon_vqtbx4_v: in EmitAArch64TblBuiltinExpr()
4763 case NEON::BI__builtin_neon_vqtbx4q_v: in EmitAArch64TblBuiltinExpr()
5066 case NEON::BI__builtin_neon_vldrq_p128: { in EmitAArch64BuiltinExpr()
5071 case NEON::BI__builtin_neon_vstrq_p128: { in EmitAArch64BuiltinExpr()
5076 case NEON::BI__builtin_neon_vcvts_u32_f32: in EmitAArch64BuiltinExpr()
5077 case NEON::BI__builtin_neon_vcvtd_u64_f64: in EmitAArch64BuiltinExpr()
5080 case NEON::BI__builtin_neon_vcvts_s32_f32: in EmitAArch64BuiltinExpr()
5081 case NEON::BI__builtin_neon_vcvtd_s64_f64: { in EmitAArch64BuiltinExpr()
5091 case NEON::BI__builtin_neon_vcvts_f32_u32: in EmitAArch64BuiltinExpr()
5092 case NEON::BI__builtin_neon_vcvtd_f64_u64: in EmitAArch64BuiltinExpr()
5095 case NEON::BI__builtin_neon_vcvts_f32_s32: in EmitAArch64BuiltinExpr()
5096 case NEON::BI__builtin_neon_vcvtd_f64_s64: { in EmitAArch64BuiltinExpr()
5106 case NEON::BI__builtin_neon_vpaddd_s64: { in EmitAArch64BuiltinExpr()
5118 case NEON::BI__builtin_neon_vpaddd_f64: { in EmitAArch64BuiltinExpr()
5131 case NEON::BI__builtin_neon_vpadds_f32: { in EmitAArch64BuiltinExpr()
5144 case NEON::BI__builtin_neon_vceqzd_s64: in EmitAArch64BuiltinExpr()
5145 case NEON::BI__builtin_neon_vceqzd_f64: in EmitAArch64BuiltinExpr()
5146 case NEON::BI__builtin_neon_vceqzs_f32: in EmitAArch64BuiltinExpr()
5151 case NEON::BI__builtin_neon_vcgezd_s64: in EmitAArch64BuiltinExpr()
5152 case NEON::BI__builtin_neon_vcgezd_f64: in EmitAArch64BuiltinExpr()
5153 case NEON::BI__builtin_neon_vcgezs_f32: in EmitAArch64BuiltinExpr()
5158 case NEON::BI__builtin_neon_vclezd_s64: in EmitAArch64BuiltinExpr()
5159 case NEON::BI__builtin_neon_vclezd_f64: in EmitAArch64BuiltinExpr()
5160 case NEON::BI__builtin_neon_vclezs_f32: in EmitAArch64BuiltinExpr()
5165 case NEON::BI__builtin_neon_vcgtzd_s64: in EmitAArch64BuiltinExpr()
5166 case NEON::BI__builtin_neon_vcgtzd_f64: in EmitAArch64BuiltinExpr()
5167 case NEON::BI__builtin_neon_vcgtzs_f32: in EmitAArch64BuiltinExpr()
5172 case NEON::BI__builtin_neon_vcltzd_s64: in EmitAArch64BuiltinExpr()
5173 case NEON::BI__builtin_neon_vcltzd_f64: in EmitAArch64BuiltinExpr()
5174 case NEON::BI__builtin_neon_vcltzs_f32: in EmitAArch64BuiltinExpr()
5180 case NEON::BI__builtin_neon_vceqzd_u64: { in EmitAArch64BuiltinExpr()
5187 case NEON::BI__builtin_neon_vceqd_f64: in EmitAArch64BuiltinExpr()
5188 case NEON::BI__builtin_neon_vcled_f64: in EmitAArch64BuiltinExpr()
5189 case NEON::BI__builtin_neon_vcltd_f64: in EmitAArch64BuiltinExpr()
5190 case NEON::BI__builtin_neon_vcged_f64: in EmitAArch64BuiltinExpr()
5191 case NEON::BI__builtin_neon_vcgtd_f64: { in EmitAArch64BuiltinExpr()
5195 case NEON::BI__builtin_neon_vceqd_f64: P = llvm::FCmpInst::FCMP_OEQ; break; in EmitAArch64BuiltinExpr()
5196 case NEON::BI__builtin_neon_vcled_f64: P = llvm::FCmpInst::FCMP_OLE; break; in EmitAArch64BuiltinExpr()
5197 case NEON::BI__builtin_neon_vcltd_f64: P = llvm::FCmpInst::FCMP_OLT; break; in EmitAArch64BuiltinExpr()
5198 case NEON::BI__builtin_neon_vcged_f64: P = llvm::FCmpInst::FCMP_OGE; break; in EmitAArch64BuiltinExpr()
5199 case NEON::BI__builtin_neon_vcgtd_f64: P = llvm::FCmpInst::FCMP_OGT; break; in EmitAArch64BuiltinExpr()
5207 case NEON::BI__builtin_neon_vceqs_f32: in EmitAArch64BuiltinExpr()
5208 case NEON::BI__builtin_neon_vcles_f32: in EmitAArch64BuiltinExpr()
5209 case NEON::BI__builtin_neon_vclts_f32: in EmitAArch64BuiltinExpr()
5210 case NEON::BI__builtin_neon_vcges_f32: in EmitAArch64BuiltinExpr()
5211 case NEON::BI__builtin_neon_vcgts_f32: { in EmitAArch64BuiltinExpr()
5215 case NEON::BI__builtin_neon_vceqs_f32: P = llvm::FCmpInst::FCMP_OEQ; break; in EmitAArch64BuiltinExpr()
5216 case NEON::BI__builtin_neon_vcles_f32: P = llvm::FCmpInst::FCMP_OLE; break; in EmitAArch64BuiltinExpr()
5217 case NEON::BI__builtin_neon_vclts_f32: P = llvm::FCmpInst::FCMP_OLT; break; in EmitAArch64BuiltinExpr()
5218 case NEON::BI__builtin_neon_vcges_f32: P = llvm::FCmpInst::FCMP_OGE; break; in EmitAArch64BuiltinExpr()
5219 case NEON::BI__builtin_neon_vcgts_f32: P = llvm::FCmpInst::FCMP_OGT; break; in EmitAArch64BuiltinExpr()
5227 case NEON::BI__builtin_neon_vceqd_s64: in EmitAArch64BuiltinExpr()
5228 case NEON::BI__builtin_neon_vceqd_u64: in EmitAArch64BuiltinExpr()
5229 case NEON::BI__builtin_neon_vcgtd_s64: in EmitAArch64BuiltinExpr()
5230 case NEON::BI__builtin_neon_vcgtd_u64: in EmitAArch64BuiltinExpr()
5231 case NEON::BI__builtin_neon_vcltd_s64: in EmitAArch64BuiltinExpr()
5232 case NEON::BI__builtin_neon_vcltd_u64: in EmitAArch64BuiltinExpr()
5233 case NEON::BI__builtin_neon_vcged_u64: in EmitAArch64BuiltinExpr()
5234 case NEON::BI__builtin_neon_vcged_s64: in EmitAArch64BuiltinExpr()
5235 case NEON::BI__builtin_neon_vcled_u64: in EmitAArch64BuiltinExpr()
5236 case NEON::BI__builtin_neon_vcled_s64: { in EmitAArch64BuiltinExpr()
5240 case NEON::BI__builtin_neon_vceqd_s64: in EmitAArch64BuiltinExpr()
5241 case NEON::BI__builtin_neon_vceqd_u64:P = llvm::ICmpInst::ICMP_EQ;break; in EmitAArch64BuiltinExpr()
5242 case NEON::BI__builtin_neon_vcgtd_s64:P = llvm::ICmpInst::ICMP_SGT;break; in EmitAArch64BuiltinExpr()
5243 case NEON::BI__builtin_neon_vcgtd_u64:P = llvm::ICmpInst::ICMP_UGT;break; in EmitAArch64BuiltinExpr()
5244 case NEON::BI__builtin_neon_vcltd_s64:P = llvm::ICmpInst::ICMP_SLT;break; in EmitAArch64BuiltinExpr()
5245 case NEON::BI__builtin_neon_vcltd_u64:P = llvm::ICmpInst::ICMP_ULT;break; in EmitAArch64BuiltinExpr()
5246 case NEON::BI__builtin_neon_vcged_u64:P = llvm::ICmpInst::ICMP_UGE;break; in EmitAArch64BuiltinExpr()
5247 case NEON::BI__builtin_neon_vcged_s64:P = llvm::ICmpInst::ICMP_SGE;break; in EmitAArch64BuiltinExpr()
5248 case NEON::BI__builtin_neon_vcled_u64:P = llvm::ICmpInst::ICMP_ULE;break; in EmitAArch64BuiltinExpr()
5249 case NEON::BI__builtin_neon_vcled_s64:P = llvm::ICmpInst::ICMP_SLE;break; in EmitAArch64BuiltinExpr()
5257 case NEON::BI__builtin_neon_vtstd_s64: in EmitAArch64BuiltinExpr()
5258 case NEON::BI__builtin_neon_vtstd_u64: { in EmitAArch64BuiltinExpr()
5267 case NEON::BI__builtin_neon_vset_lane_i8: in EmitAArch64BuiltinExpr()
5268 case NEON::BI__builtin_neon_vset_lane_i16: in EmitAArch64BuiltinExpr()
5269 case NEON::BI__builtin_neon_vset_lane_i32: in EmitAArch64BuiltinExpr()
5270 case NEON::BI__builtin_neon_vset_lane_i64: in EmitAArch64BuiltinExpr()
5271 case NEON::BI__builtin_neon_vset_lane_f32: in EmitAArch64BuiltinExpr()
5272 case NEON::BI__builtin_neon_vsetq_lane_i8: in EmitAArch64BuiltinExpr()
5273 case NEON::BI__builtin_neon_vsetq_lane_i16: in EmitAArch64BuiltinExpr()
5274 case NEON::BI__builtin_neon_vsetq_lane_i32: in EmitAArch64BuiltinExpr()
5275 case NEON::BI__builtin_neon_vsetq_lane_i64: in EmitAArch64BuiltinExpr()
5276 case NEON::BI__builtin_neon_vsetq_lane_f32: in EmitAArch64BuiltinExpr()
5279 case NEON::BI__builtin_neon_vset_lane_f64: in EmitAArch64BuiltinExpr()
5285 case NEON::BI__builtin_neon_vsetq_lane_f64: in EmitAArch64BuiltinExpr()
5292 case NEON::BI__builtin_neon_vget_lane_i8: in EmitAArch64BuiltinExpr()
5293 case NEON::BI__builtin_neon_vdupb_lane_i8: in EmitAArch64BuiltinExpr()
5297 case NEON::BI__builtin_neon_vgetq_lane_i8: in EmitAArch64BuiltinExpr()
5298 case NEON::BI__builtin_neon_vdupb_laneq_i8: in EmitAArch64BuiltinExpr()
5302 case NEON::BI__builtin_neon_vget_lane_i16: in EmitAArch64BuiltinExpr()
5303 case NEON::BI__builtin_neon_vduph_lane_i16: in EmitAArch64BuiltinExpr()
5307 case NEON::BI__builtin_neon_vgetq_lane_i16: in EmitAArch64BuiltinExpr()
5308 case NEON::BI__builtin_neon_vduph_laneq_i16: in EmitAArch64BuiltinExpr()
5312 case NEON::BI__builtin_neon_vget_lane_i32: in EmitAArch64BuiltinExpr()
5313 case NEON::BI__builtin_neon_vdups_lane_i32: in EmitAArch64BuiltinExpr()
5317 case NEON::BI__builtin_neon_vdups_lane_f32: in EmitAArch64BuiltinExpr()
5322 case NEON::BI__builtin_neon_vgetq_lane_i32: in EmitAArch64BuiltinExpr()
5323 case NEON::BI__builtin_neon_vdups_laneq_i32: in EmitAArch64BuiltinExpr()
5327 case NEON::BI__builtin_neon_vget_lane_i64: in EmitAArch64BuiltinExpr()
5328 case NEON::BI__builtin_neon_vdupd_lane_i64: in EmitAArch64BuiltinExpr()
5332 case NEON::BI__builtin_neon_vdupd_lane_f64: in EmitAArch64BuiltinExpr()
5337 case NEON::BI__builtin_neon_vgetq_lane_i64: in EmitAArch64BuiltinExpr()
5338 case NEON::BI__builtin_neon_vdupd_laneq_i64: in EmitAArch64BuiltinExpr()
5342 case NEON::BI__builtin_neon_vget_lane_f32: in EmitAArch64BuiltinExpr()
5347 case NEON::BI__builtin_neon_vget_lane_f64: in EmitAArch64BuiltinExpr()
5352 case NEON::BI__builtin_neon_vgetq_lane_f32: in EmitAArch64BuiltinExpr()
5353 case NEON::BI__builtin_neon_vdups_laneq_f32: in EmitAArch64BuiltinExpr()
5358 case NEON::BI__builtin_neon_vgetq_lane_f64: in EmitAArch64BuiltinExpr()
5359 case NEON::BI__builtin_neon_vdupd_laneq_f64: in EmitAArch64BuiltinExpr()
5364 case NEON::BI__builtin_neon_vaddd_s64: in EmitAArch64BuiltinExpr()
5365 case NEON::BI__builtin_neon_vaddd_u64: in EmitAArch64BuiltinExpr()
5367 case NEON::BI__builtin_neon_vsubd_s64: in EmitAArch64BuiltinExpr()
5368 case NEON::BI__builtin_neon_vsubd_u64: in EmitAArch64BuiltinExpr()
5370 case NEON::BI__builtin_neon_vqdmlalh_s16: in EmitAArch64BuiltinExpr()
5371 case NEON::BI__builtin_neon_vqdmlslh_s16: { in EmitAArch64BuiltinExpr()
5381 unsigned AccumInt = BuiltinID == NEON::BI__builtin_neon_vqdmlalh_s16 in EmitAArch64BuiltinExpr()
5386 case NEON::BI__builtin_neon_vqshlud_n_s64: { in EmitAArch64BuiltinExpr()
5392 case NEON::BI__builtin_neon_vqshld_n_u64: in EmitAArch64BuiltinExpr()
5393 case NEON::BI__builtin_neon_vqshld_n_s64: { in EmitAArch64BuiltinExpr()
5394 unsigned Int = BuiltinID == NEON::BI__builtin_neon_vqshld_n_u64 in EmitAArch64BuiltinExpr()
5401 case NEON::BI__builtin_neon_vrshrd_n_u64: in EmitAArch64BuiltinExpr()
5402 case NEON::BI__builtin_neon_vrshrd_n_s64: { in EmitAArch64BuiltinExpr()
5403 unsigned Int = BuiltinID == NEON::BI__builtin_neon_vrshrd_n_u64 in EmitAArch64BuiltinExpr()
5411 case NEON::BI__builtin_neon_vrsrad_n_u64: in EmitAArch64BuiltinExpr()
5412 case NEON::BI__builtin_neon_vrsrad_n_s64: { in EmitAArch64BuiltinExpr()
5413 unsigned Int = BuiltinID == NEON::BI__builtin_neon_vrsrad_n_u64 in EmitAArch64BuiltinExpr()
5422 case NEON::BI__builtin_neon_vshld_n_s64: in EmitAArch64BuiltinExpr()
5423 case NEON::BI__builtin_neon_vshld_n_u64: { in EmitAArch64BuiltinExpr()
5428 case NEON::BI__builtin_neon_vshrd_n_s64: { in EmitAArch64BuiltinExpr()
5435 case NEON::BI__builtin_neon_vshrd_n_u64: { in EmitAArch64BuiltinExpr()
5444 case NEON::BI__builtin_neon_vsrad_n_s64: { in EmitAArch64BuiltinExpr()
5452 case NEON::BI__builtin_neon_vsrad_n_u64: { in EmitAArch64BuiltinExpr()
5463 case NEON::BI__builtin_neon_vqdmlalh_lane_s16: in EmitAArch64BuiltinExpr()
5464 case NEON::BI__builtin_neon_vqdmlalh_laneq_s16: in EmitAArch64BuiltinExpr()
5465 case NEON::BI__builtin_neon_vqdmlslh_lane_s16: in EmitAArch64BuiltinExpr()
5466 case NEON::BI__builtin_neon_vqdmlslh_laneq_s16: { in EmitAArch64BuiltinExpr()
5479 unsigned AccInt = (BuiltinID == NEON::BI__builtin_neon_vqdmlalh_lane_s16 || in EmitAArch64BuiltinExpr()
5480 BuiltinID == NEON::BI__builtin_neon_vqdmlalh_laneq_s16) in EmitAArch64BuiltinExpr()
5485 case NEON::BI__builtin_neon_vqdmlals_s32: in EmitAArch64BuiltinExpr()
5486 case NEON::BI__builtin_neon_vqdmlsls_s32: { in EmitAArch64BuiltinExpr()
5494 unsigned AccumInt = BuiltinID == NEON::BI__builtin_neon_vqdmlals_s32 in EmitAArch64BuiltinExpr()
5499 case NEON::BI__builtin_neon_vqdmlals_lane_s32: in EmitAArch64BuiltinExpr()
5500 case NEON::BI__builtin_neon_vqdmlals_laneq_s32: in EmitAArch64BuiltinExpr()
5501 case NEON::BI__builtin_neon_vqdmlsls_lane_s32: in EmitAArch64BuiltinExpr()
5502 case NEON::BI__builtin_neon_vqdmlsls_laneq_s32: { in EmitAArch64BuiltinExpr()
5513 unsigned AccInt = (BuiltinID == NEON::BI__builtin_neon_vqdmlals_lane_s32 || in EmitAArch64BuiltinExpr()
5514 BuiltinID == NEON::BI__builtin_neon_vqdmlals_laneq_s32) in EmitAArch64BuiltinExpr()
5543 case NEON::BI__builtin_neon_vbsl_v: in EmitAArch64BuiltinExpr()
5544 case NEON::BI__builtin_neon_vbslq_v: { in EmitAArch64BuiltinExpr()
5555 case NEON::BI__builtin_neon_vfma_lane_v: in EmitAArch64BuiltinExpr()
5556 case NEON::BI__builtin_neon_vfmaq_lane_v: { // Only used for FP types in EmitAArch64BuiltinExpr()
5567 llvm::Type *SourceTy = BuiltinID == NEON::BI__builtin_neon_vfmaq_lane_v ? in EmitAArch64BuiltinExpr()
5579 case NEON::BI__builtin_neon_vfma_laneq_v: { in EmitAArch64BuiltinExpr()
5606 case NEON::BI__builtin_neon_vfmaq_laneq_v: { in EmitAArch64BuiltinExpr()
5615 case NEON::BI__builtin_neon_vfmas_lane_f32: in EmitAArch64BuiltinExpr()
5616 case NEON::BI__builtin_neon_vfmas_laneq_f32: in EmitAArch64BuiltinExpr()
5617 case NEON::BI__builtin_neon_vfmad_lane_f64: in EmitAArch64BuiltinExpr()
5618 case NEON::BI__builtin_neon_vfmad_laneq_f64: { in EmitAArch64BuiltinExpr()
5625 case NEON::BI__builtin_neon_vmull_v: in EmitAArch64BuiltinExpr()
5630 case NEON::BI__builtin_neon_vmax_v: in EmitAArch64BuiltinExpr()
5631 case NEON::BI__builtin_neon_vmaxq_v: in EmitAArch64BuiltinExpr()
5636 case NEON::BI__builtin_neon_vmin_v: in EmitAArch64BuiltinExpr()
5637 case NEON::BI__builtin_neon_vminq_v: in EmitAArch64BuiltinExpr()
5642 case NEON::BI__builtin_neon_vabd_v: in EmitAArch64BuiltinExpr()
5643 case NEON::BI__builtin_neon_vabdq_v: in EmitAArch64BuiltinExpr()
5648 case NEON::BI__builtin_neon_vpadal_v: in EmitAArch64BuiltinExpr()
5649 case NEON::BI__builtin_neon_vpadalq_v: { in EmitAArch64BuiltinExpr()
5664 case NEON::BI__builtin_neon_vpmin_v: in EmitAArch64BuiltinExpr()
5665 case NEON::BI__builtin_neon_vpminq_v: in EmitAArch64BuiltinExpr()
5670 case NEON::BI__builtin_neon_vpmax_v: in EmitAArch64BuiltinExpr()
5671 case NEON::BI__builtin_neon_vpmaxq_v: in EmitAArch64BuiltinExpr()
5676 case NEON::BI__builtin_neon_vminnm_v: in EmitAArch64BuiltinExpr()
5677 case NEON::BI__builtin_neon_vminnmq_v: in EmitAArch64BuiltinExpr()
5680 case NEON::BI__builtin_neon_vmaxnm_v: in EmitAArch64BuiltinExpr()
5681 case NEON::BI__builtin_neon_vmaxnmq_v: in EmitAArch64BuiltinExpr()
5684 case NEON::BI__builtin_neon_vrecpss_f32: { in EmitAArch64BuiltinExpr()
5689 case NEON::BI__builtin_neon_vrecpsd_f64: { in EmitAArch64BuiltinExpr()
5694 case NEON::BI__builtin_neon_vqshrun_n_v: in EmitAArch64BuiltinExpr()
5697 case NEON::BI__builtin_neon_vqrshrun_n_v: in EmitAArch64BuiltinExpr()
5700 case NEON::BI__builtin_neon_vqshrn_n_v: in EmitAArch64BuiltinExpr()
5703 case NEON::BI__builtin_neon_vrshrn_n_v: in EmitAArch64BuiltinExpr()
5706 case NEON::BI__builtin_neon_vqrshrn_n_v: in EmitAArch64BuiltinExpr()
5709 case NEON::BI__builtin_neon_vrnda_v: in EmitAArch64BuiltinExpr()
5710 case NEON::BI__builtin_neon_vrndaq_v: { in EmitAArch64BuiltinExpr()
5714 case NEON::BI__builtin_neon_vrndi_v: in EmitAArch64BuiltinExpr()
5715 case NEON::BI__builtin_neon_vrndiq_v: { in EmitAArch64BuiltinExpr()
5719 case NEON::BI__builtin_neon_vrndm_v: in EmitAArch64BuiltinExpr()
5720 case NEON::BI__builtin_neon_vrndmq_v: { in EmitAArch64BuiltinExpr()
5724 case NEON::BI__builtin_neon_vrndn_v: in EmitAArch64BuiltinExpr()
5725 case NEON::BI__builtin_neon_vrndnq_v: { in EmitAArch64BuiltinExpr()
5729 case NEON::BI__builtin_neon_vrndp_v: in EmitAArch64BuiltinExpr()
5730 case NEON::BI__builtin_neon_vrndpq_v: { in EmitAArch64BuiltinExpr()
5734 case NEON::BI__builtin_neon_vrndx_v: in EmitAArch64BuiltinExpr()
5735 case NEON::BI__builtin_neon_vrndxq_v: { in EmitAArch64BuiltinExpr()
5739 case NEON::BI__builtin_neon_vrnd_v: in EmitAArch64BuiltinExpr()
5740 case NEON::BI__builtin_neon_vrndq_v: { in EmitAArch64BuiltinExpr()
5744 case NEON::BI__builtin_neon_vceqz_v: in EmitAArch64BuiltinExpr()
5745 case NEON::BI__builtin_neon_vceqzq_v: in EmitAArch64BuiltinExpr()
5748 case NEON::BI__builtin_neon_vcgez_v: in EmitAArch64BuiltinExpr()
5749 case NEON::BI__builtin_neon_vcgezq_v: in EmitAArch64BuiltinExpr()
5752 case NEON::BI__builtin_neon_vclez_v: in EmitAArch64BuiltinExpr()
5753 case NEON::BI__builtin_neon_vclezq_v: in EmitAArch64BuiltinExpr()
5756 case NEON::BI__builtin_neon_vcgtz_v: in EmitAArch64BuiltinExpr()
5757 case NEON::BI__builtin_neon_vcgtzq_v: in EmitAArch64BuiltinExpr()
5760 case NEON::BI__builtin_neon_vcltz_v: in EmitAArch64BuiltinExpr()
5761 case NEON::BI__builtin_neon_vcltzq_v: in EmitAArch64BuiltinExpr()
5764 case NEON::BI__builtin_neon_vcvt_f64_v: in EmitAArch64BuiltinExpr()
5765 case NEON::BI__builtin_neon_vcvtq_f64_v: in EmitAArch64BuiltinExpr()
5770 case NEON::BI__builtin_neon_vcvt_f64_f32: { in EmitAArch64BuiltinExpr()
5778 case NEON::BI__builtin_neon_vcvt_f32_f64: { in EmitAArch64BuiltinExpr()
5786 case NEON::BI__builtin_neon_vcvt_s32_v: in EmitAArch64BuiltinExpr()
5787 case NEON::BI__builtin_neon_vcvt_u32_v: in EmitAArch64BuiltinExpr()
5788 case NEON::BI__builtin_neon_vcvt_s64_v: in EmitAArch64BuiltinExpr()
5789 case NEON::BI__builtin_neon_vcvt_u64_v: in EmitAArch64BuiltinExpr()
5790 case NEON::BI__builtin_neon_vcvtq_s32_v: in EmitAArch64BuiltinExpr()
5791 case NEON::BI__builtin_neon_vcvtq_u32_v: in EmitAArch64BuiltinExpr()
5792 case NEON::BI__builtin_neon_vcvtq_s64_v: in EmitAArch64BuiltinExpr()
5793 case NEON::BI__builtin_neon_vcvtq_u64_v: { in EmitAArch64BuiltinExpr()
5799 case NEON::BI__builtin_neon_vcvta_s32_v: in EmitAArch64BuiltinExpr()
5800 case NEON::BI__builtin_neon_vcvtaq_s32_v: in EmitAArch64BuiltinExpr()
5801 case NEON::BI__builtin_neon_vcvta_u32_v: in EmitAArch64BuiltinExpr()
5802 case NEON::BI__builtin_neon_vcvtaq_u32_v: in EmitAArch64BuiltinExpr()
5803 case NEON::BI__builtin_neon_vcvta_s64_v: in EmitAArch64BuiltinExpr()
5804 case NEON::BI__builtin_neon_vcvtaq_s64_v: in EmitAArch64BuiltinExpr()
5805 case NEON::BI__builtin_neon_vcvta_u64_v: in EmitAArch64BuiltinExpr()
5806 case NEON::BI__builtin_neon_vcvtaq_u64_v: { in EmitAArch64BuiltinExpr()
5811 case NEON::BI__builtin_neon_vcvtm_s32_v: in EmitAArch64BuiltinExpr()
5812 case NEON::BI__builtin_neon_vcvtmq_s32_v: in EmitAArch64BuiltinExpr()
5813 case NEON::BI__builtin_neon_vcvtm_u32_v: in EmitAArch64BuiltinExpr()
5814 case NEON::BI__builtin_neon_vcvtmq_u32_v: in EmitAArch64BuiltinExpr()
5815 case NEON::BI__builtin_neon_vcvtm_s64_v: in EmitAArch64BuiltinExpr()
5816 case NEON::BI__builtin_neon_vcvtmq_s64_v: in EmitAArch64BuiltinExpr()
5817 case NEON::BI__builtin_neon_vcvtm_u64_v: in EmitAArch64BuiltinExpr()
5818 case NEON::BI__builtin_neon_vcvtmq_u64_v: { in EmitAArch64BuiltinExpr()
5823 case NEON::BI__builtin_neon_vcvtn_s32_v: in EmitAArch64BuiltinExpr()
5824 case NEON::BI__builtin_neon_vcvtnq_s32_v: in EmitAArch64BuiltinExpr()
5825 case NEON::BI__builtin_neon_vcvtn_u32_v: in EmitAArch64BuiltinExpr()
5826 case NEON::BI__builtin_neon_vcvtnq_u32_v: in EmitAArch64BuiltinExpr()
5827 case NEON::BI__builtin_neon_vcvtn_s64_v: in EmitAArch64BuiltinExpr()
5828 case NEON::BI__builtin_neon_vcvtnq_s64_v: in EmitAArch64BuiltinExpr()
5829 case NEON::BI__builtin_neon_vcvtn_u64_v: in EmitAArch64BuiltinExpr()
5830 case NEON::BI__builtin_neon_vcvtnq_u64_v: { in EmitAArch64BuiltinExpr()
5835 case NEON::BI__builtin_neon_vcvtp_s32_v: in EmitAArch64BuiltinExpr()
5836 case NEON::BI__builtin_neon_vcvtpq_s32_v: in EmitAArch64BuiltinExpr()
5837 case NEON::BI__builtin_neon_vcvtp_u32_v: in EmitAArch64BuiltinExpr()
5838 case NEON::BI__builtin_neon_vcvtpq_u32_v: in EmitAArch64BuiltinExpr()
5839 case NEON::BI__builtin_neon_vcvtp_s64_v: in EmitAArch64BuiltinExpr()
5840 case NEON::BI__builtin_neon_vcvtpq_s64_v: in EmitAArch64BuiltinExpr()
5841 case NEON::BI__builtin_neon_vcvtp_u64_v: in EmitAArch64BuiltinExpr()
5842 case NEON::BI__builtin_neon_vcvtpq_u64_v: { in EmitAArch64BuiltinExpr()
5847 case NEON::BI__builtin_neon_vmulx_v: in EmitAArch64BuiltinExpr()
5848 case NEON::BI__builtin_neon_vmulxq_v: { in EmitAArch64BuiltinExpr()
5852 case NEON::BI__builtin_neon_vmul_lane_v: in EmitAArch64BuiltinExpr()
5853 case NEON::BI__builtin_neon_vmul_laneq_v: { in EmitAArch64BuiltinExpr()
5856 if (BuiltinID == NEON::BI__builtin_neon_vmul_laneq_v) in EmitAArch64BuiltinExpr()
5866 case NEON::BI__builtin_neon_vnegd_s64: in EmitAArch64BuiltinExpr()
5868 case NEON::BI__builtin_neon_vpmaxnm_v: in EmitAArch64BuiltinExpr()
5869 case NEON::BI__builtin_neon_vpmaxnmq_v: { in EmitAArch64BuiltinExpr()
5873 case NEON::BI__builtin_neon_vpminnm_v: in EmitAArch64BuiltinExpr()
5874 case NEON::BI__builtin_neon_vpminnmq_v: { in EmitAArch64BuiltinExpr()
5878 case NEON::BI__builtin_neon_vsqrt_v: in EmitAArch64BuiltinExpr()
5879 case NEON::BI__builtin_neon_vsqrtq_v: { in EmitAArch64BuiltinExpr()
5884 case NEON::BI__builtin_neon_vrbit_v: in EmitAArch64BuiltinExpr()
5885 case NEON::BI__builtin_neon_vrbitq_v: { in EmitAArch64BuiltinExpr()
5889 case NEON::BI__builtin_neon_vaddv_u8: in EmitAArch64BuiltinExpr()
5893 case NEON::BI__builtin_neon_vaddv_s8: { in EmitAArch64BuiltinExpr()
5902 case NEON::BI__builtin_neon_vaddv_u16: in EmitAArch64BuiltinExpr()
5905 case NEON::BI__builtin_neon_vaddv_s16: { in EmitAArch64BuiltinExpr()
5914 case NEON::BI__builtin_neon_vaddvq_u8: in EmitAArch64BuiltinExpr()
5917 case NEON::BI__builtin_neon_vaddvq_s8: { in EmitAArch64BuiltinExpr()
5926 case NEON::BI__builtin_neon_vaddvq_u16: in EmitAArch64BuiltinExpr()
5929 case NEON::BI__builtin_neon_vaddvq_s16: { in EmitAArch64BuiltinExpr()
5938 case NEON::BI__builtin_neon_vmaxv_u8: { in EmitAArch64BuiltinExpr()
5947 case NEON::BI__builtin_neon_vmaxv_u16: { in EmitAArch64BuiltinExpr()
5956 case NEON::BI__builtin_neon_vmaxvq_u8: { in EmitAArch64BuiltinExpr()
5965 case NEON::BI__builtin_neon_vmaxvq_u16: { in EmitAArch64BuiltinExpr()
5974 case NEON::BI__builtin_neon_vmaxv_s8: { in EmitAArch64BuiltinExpr()
5983 case NEON::BI__builtin_neon_vmaxv_s16: { in EmitAArch64BuiltinExpr()
5992 case NEON::BI__builtin_neon_vmaxvq_s8: { in EmitAArch64BuiltinExpr()
6001 case NEON::BI__builtin_neon_vmaxvq_s16: { in EmitAArch64BuiltinExpr()
6010 case NEON::BI__builtin_neon_vminv_u8: { in EmitAArch64BuiltinExpr()
6019 case NEON::BI__builtin_neon_vminv_u16: { in EmitAArch64BuiltinExpr()
6028 case NEON::BI__builtin_neon_vminvq_u8: { in EmitAArch64BuiltinExpr()
6037 case NEON::BI__builtin_neon_vminvq_u16: { in EmitAArch64BuiltinExpr()
6046 case NEON::BI__builtin_neon_vminv_s8: { in EmitAArch64BuiltinExpr()
6055 case NEON::BI__builtin_neon_vminv_s16: { in EmitAArch64BuiltinExpr()
6064 case NEON::BI__builtin_neon_vminvq_s8: { in EmitAArch64BuiltinExpr()
6073 case NEON::BI__builtin_neon_vminvq_s16: { in EmitAArch64BuiltinExpr()
6082 case NEON::BI__builtin_neon_vmul_n_f64: { in EmitAArch64BuiltinExpr()
6087 case NEON::BI__builtin_neon_vaddlv_u8: { in EmitAArch64BuiltinExpr()
6096 case NEON::BI__builtin_neon_vaddlv_u16: { in EmitAArch64BuiltinExpr()
6104 case NEON::BI__builtin_neon_vaddlvq_u8: { in EmitAArch64BuiltinExpr()
6113 case NEON::BI__builtin_neon_vaddlvq_u16: { in EmitAArch64BuiltinExpr()
6121 case NEON::BI__builtin_neon_vaddlv_s8: { in EmitAArch64BuiltinExpr()
6130 case NEON::BI__builtin_neon_vaddlv_s16: { in EmitAArch64BuiltinExpr()
6138 case NEON::BI__builtin_neon_vaddlvq_s8: { in EmitAArch64BuiltinExpr()
6147 case NEON::BI__builtin_neon_vaddlvq_s16: { in EmitAArch64BuiltinExpr()
6155 case NEON::BI__builtin_neon_vsri_n_v: in EmitAArch64BuiltinExpr()
6156 case NEON::BI__builtin_neon_vsriq_n_v: { in EmitAArch64BuiltinExpr()
6161 case NEON::BI__builtin_neon_vsli_n_v: in EmitAArch64BuiltinExpr()
6162 case NEON::BI__builtin_neon_vsliq_n_v: { in EmitAArch64BuiltinExpr()
6167 case NEON::BI__builtin_neon_vsra_n_v: in EmitAArch64BuiltinExpr()
6168 case NEON::BI__builtin_neon_vsraq_n_v: in EmitAArch64BuiltinExpr()
6172 case NEON::BI__builtin_neon_vrsra_n_v: in EmitAArch64BuiltinExpr()
6173 case NEON::BI__builtin_neon_vrsraq_n_v: { in EmitAArch64BuiltinExpr()
6185 case NEON::BI__builtin_neon_vld1_x2_v: in EmitAArch64BuiltinExpr()
6186 case NEON::BI__builtin_neon_vld1q_x2_v: in EmitAArch64BuiltinExpr()
6187 case NEON::BI__builtin_neon_vld1_x3_v: in EmitAArch64BuiltinExpr()
6188 case NEON::BI__builtin_neon_vld1q_x3_v: in EmitAArch64BuiltinExpr()
6189 case NEON::BI__builtin_neon_vld1_x4_v: in EmitAArch64BuiltinExpr()
6190 case NEON::BI__builtin_neon_vld1q_x4_v: { in EmitAArch64BuiltinExpr()
6196 case NEON::BI__builtin_neon_vld1_x2_v: in EmitAArch64BuiltinExpr()
6197 case NEON::BI__builtin_neon_vld1q_x2_v: in EmitAArch64BuiltinExpr()
6200 case NEON::BI__builtin_neon_vld1_x3_v: in EmitAArch64BuiltinExpr()
6201 case NEON::BI__builtin_neon_vld1q_x3_v: in EmitAArch64BuiltinExpr()
6204 case NEON::BI__builtin_neon_vld1_x4_v: in EmitAArch64BuiltinExpr()
6205 case NEON::BI__builtin_neon_vld1q_x4_v: in EmitAArch64BuiltinExpr()
6215 case NEON::BI__builtin_neon_vst1_x2_v: in EmitAArch64BuiltinExpr()
6216 case NEON::BI__builtin_neon_vst1q_x2_v: in EmitAArch64BuiltinExpr()
6217 case NEON::BI__builtin_neon_vst1_x3_v: in EmitAArch64BuiltinExpr()
6218 case NEON::BI__builtin_neon_vst1q_x3_v: in EmitAArch64BuiltinExpr()
6219 case NEON::BI__builtin_neon_vst1_x4_v: in EmitAArch64BuiltinExpr()
6220 case NEON::BI__builtin_neon_vst1q_x4_v: { in EmitAArch64BuiltinExpr()
6225 case NEON::BI__builtin_neon_vst1_x2_v: in EmitAArch64BuiltinExpr()
6226 case NEON::BI__builtin_neon_vst1q_x2_v: in EmitAArch64BuiltinExpr()
6229 case NEON::BI__builtin_neon_vst1_x3_v: in EmitAArch64BuiltinExpr()
6230 case NEON::BI__builtin_neon_vst1q_x3_v: in EmitAArch64BuiltinExpr()
6233 case NEON::BI__builtin_neon_vst1_x4_v: in EmitAArch64BuiltinExpr()
6234 case NEON::BI__builtin_neon_vst1q_x4_v: in EmitAArch64BuiltinExpr()
6241 case NEON::BI__builtin_neon_vld1_v: in EmitAArch64BuiltinExpr()
6242 case NEON::BI__builtin_neon_vld1q_v: in EmitAArch64BuiltinExpr()
6245 case NEON::BI__builtin_neon_vst1_v: in EmitAArch64BuiltinExpr()
6246 case NEON::BI__builtin_neon_vst1q_v: in EmitAArch64BuiltinExpr()
6250 case NEON::BI__builtin_neon_vld1_lane_v: in EmitAArch64BuiltinExpr()
6251 case NEON::BI__builtin_neon_vld1q_lane_v: in EmitAArch64BuiltinExpr()
6257 case NEON::BI__builtin_neon_vld1_dup_v: in EmitAArch64BuiltinExpr()
6258 case NEON::BI__builtin_neon_vld1q_dup_v: { in EmitAArch64BuiltinExpr()
6267 case NEON::BI__builtin_neon_vst1_lane_v: in EmitAArch64BuiltinExpr()
6268 case NEON::BI__builtin_neon_vst1q_lane_v: in EmitAArch64BuiltinExpr()
6274 case NEON::BI__builtin_neon_vld2_v: in EmitAArch64BuiltinExpr()
6275 case NEON::BI__builtin_neon_vld2q_v: { in EmitAArch64BuiltinExpr()
6285 case NEON::BI__builtin_neon_vld3_v: in EmitAArch64BuiltinExpr()
6286 case NEON::BI__builtin_neon_vld3q_v: { in EmitAArch64BuiltinExpr()
6296 case NEON::BI__builtin_neon_vld4_v: in EmitAArch64BuiltinExpr()
6297 case NEON::BI__builtin_neon_vld4q_v: { in EmitAArch64BuiltinExpr()
6307 case NEON::BI__builtin_neon_vld2_dup_v: in EmitAArch64BuiltinExpr()
6308 case NEON::BI__builtin_neon_vld2q_dup_v: { in EmitAArch64BuiltinExpr()
6319 case NEON::BI__builtin_neon_vld3_dup_v: in EmitAArch64BuiltinExpr()
6320 case NEON::BI__builtin_neon_vld3q_dup_v: { in EmitAArch64BuiltinExpr()
6331 case NEON::BI__builtin_neon_vld4_dup_v: in EmitAArch64BuiltinExpr()
6332 case NEON::BI__builtin_neon_vld4q_dup_v: { in EmitAArch64BuiltinExpr()
6343 case NEON::BI__builtin_neon_vld2_lane_v: in EmitAArch64BuiltinExpr()
6344 case NEON::BI__builtin_neon_vld2q_lane_v: { in EmitAArch64BuiltinExpr()
6357 case NEON::BI__builtin_neon_vld3_lane_v: in EmitAArch64BuiltinExpr()
6358 case NEON::BI__builtin_neon_vld3q_lane_v: { in EmitAArch64BuiltinExpr()
6372 case NEON::BI__builtin_neon_vld4_lane_v: in EmitAArch64BuiltinExpr()
6373 case NEON::BI__builtin_neon_vld4q_lane_v: { in EmitAArch64BuiltinExpr()
6388 case NEON::BI__builtin_neon_vst2_v: in EmitAArch64BuiltinExpr()
6389 case NEON::BI__builtin_neon_vst2q_v: { in EmitAArch64BuiltinExpr()
6396 case NEON::BI__builtin_neon_vst2_lane_v: in EmitAArch64BuiltinExpr()
6397 case NEON::BI__builtin_neon_vst2q_lane_v: { in EmitAArch64BuiltinExpr()
6405 case NEON::BI__builtin_neon_vst3_v: in EmitAArch64BuiltinExpr()
6406 case NEON::BI__builtin_neon_vst3q_v: { in EmitAArch64BuiltinExpr()
6413 case NEON::BI__builtin_neon_vst3_lane_v: in EmitAArch64BuiltinExpr()
6414 case NEON::BI__builtin_neon_vst3q_lane_v: { in EmitAArch64BuiltinExpr()
6422 case NEON::BI__builtin_neon_vst4_v: in EmitAArch64BuiltinExpr()
6423 case NEON::BI__builtin_neon_vst4q_v: { in EmitAArch64BuiltinExpr()
6430 case NEON::BI__builtin_neon_vst4_lane_v: in EmitAArch64BuiltinExpr()
6431 case NEON::BI__builtin_neon_vst4q_lane_v: { in EmitAArch64BuiltinExpr()
6439 case NEON::BI__builtin_neon_vtrn_v: in EmitAArch64BuiltinExpr()
6440 case NEON::BI__builtin_neon_vtrnq_v: { in EmitAArch64BuiltinExpr()
6458 case NEON::BI__builtin_neon_vuzp_v: in EmitAArch64BuiltinExpr()
6459 case NEON::BI__builtin_neon_vuzpq_v: { in EmitAArch64BuiltinExpr()
6476 case NEON::BI__builtin_neon_vzip_v: in EmitAArch64BuiltinExpr()
6477 case NEON::BI__builtin_neon_vzipq_v: { in EmitAArch64BuiltinExpr()
6495 case NEON::BI__builtin_neon_vqtbl1q_v: { in EmitAArch64BuiltinExpr()
6499 case NEON::BI__builtin_neon_vqtbl2q_v: { in EmitAArch64BuiltinExpr()
6503 case NEON::BI__builtin_neon_vqtbl3q_v: { in EmitAArch64BuiltinExpr()
6507 case NEON::BI__builtin_neon_vqtbl4q_v: { in EmitAArch64BuiltinExpr()
6511 case NEON::BI__builtin_neon_vqtbx1q_v: { in EmitAArch64BuiltinExpr()
6515 case NEON::BI__builtin_neon_vqtbx2q_v: { in EmitAArch64BuiltinExpr()
6519 case NEON::BI__builtin_neon_vqtbx3q_v: { in EmitAArch64BuiltinExpr()
6523 case NEON::BI__builtin_neon_vqtbx4q_v: { in EmitAArch64BuiltinExpr()
6527 case NEON::BI__builtin_neon_vsqadd_v: in EmitAArch64BuiltinExpr()
6528 case NEON::BI__builtin_neon_vsqaddq_v: { in EmitAArch64BuiltinExpr()
6532 case NEON::BI__builtin_neon_vuqadd_v: in EmitAArch64BuiltinExpr()
6533 case NEON::BI__builtin_neon_vuqaddq_v: { in EmitAArch64BuiltinExpr()