Lines Matching refs:ARM
1880 return CGF.EmitARMBuiltinExpr(ARM::BI__builtin_neon_vget_lane_i8, E);
1893 return CGF.EmitARMBuiltinExpr(ARM::BI__builtin_neon_vset_lane_i8, E);
2911 // Handle ld1/st1 lane in this function a little different from ARM.
2933 // Handle ld1/st1 dup lane in this function a little different from ARM.
2975 // AArch64 builtins mapping to legacy ARM v7 builtins.
2979 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vuzp_v, E);
2981 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vuzpq_v, E);
2983 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vzip_v, E);
2985 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vzipq_v, E);
2987 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vtrn_v, E);
2989 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vtrnq_v, E);
2991 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vext_v, E);
2993 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vextq_v, E);
2995 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmul_v, E);
2997 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmulq_v, E);
2999 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vabd_v, E);
3001 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vabdq_v, E);
3003 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vfma_v, E);
3005 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vfmaq_v, E);
3007 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vbsl_v, E);
3009 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vbslq_v, E);
3011 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrsqrts_v, E);
3013 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrsqrtsq_v, E);
3015 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrecps_v, E);
3017 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrecpsq_v, E);
3022 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcale_v, E);
3035 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcage_v, E);
3050 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcalt_v, E);
3063 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcagt_v, E);
3075 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vtst_v, E);
3077 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vtstq_v, E);
3079 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vhadd_v, E);
3081 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vhaddq_v, E);
3083 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vhsub_v, E);
3085 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vhsubq_v, E);
3087 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrhadd_v, E);
3089 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrhaddq_v, E);
3091 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqadd_v, E);
3093 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqaddq_v, E);
3095 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqsub_v, E);
3097 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqsubq_v, E);
3099 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vshl_v, E);
3101 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vshlq_v, E);
3103 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqshl_v, E);
3105 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqshlq_v, E);
3107 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrshl_v, E);
3109 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrshlq_v, E);
3111 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqrshl_v, E);
3113 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqrshlq_v, E);
3115 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vaddhn_v, E);
3117 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vraddhn_v, E);
3119 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vsubhn_v, E);
3121 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrsubhn_v, E);
3123 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmull_v, E);
3125 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqdmull_v, E);
3127 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqdmlal_v, E);
3129 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqdmlsl_v, E);
3131 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmax_v, E);
3133 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmaxq_v, E);
3135 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmin_v, E);
3137 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vminq_v, E);
3139 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vpmax_v, E);
3141 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vpmin_v, E);
3143 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vpadd_v, E);
3145 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqdmulh_v, E);
3147 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqdmulhq_v, E);
3149 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqrdmulh_v, E);
3151 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqrdmulhq_v, E);
3155 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vshr_n_v, E);
3157 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vshrq_n_v, E);
3169 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vsra_n_v, E);
3171 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vsraq_n_v, E);
3188 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vshl_n_v, E);
3190 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vshlq_n_v, E);
3192 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqshl_n_v, E);
3194 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqshlq_n_v, E);
3247 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmovl_v, E);
3249 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvt_n_f32_v, E);
3251 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvtq_n_f32_v, E);
3263 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvt_n_s32_v, E);
3265 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvtq_n_s32_v, E);
3267 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvt_n_u32_v, E);
3269 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvtq_n_u32_v, E);
3285 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld1_v, E);
3287 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld1q_v, E);
3289 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld2_v, E);
3291 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld2q_v, E);
3293 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld3_v, E);
3295 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld3q_v, E);
3297 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld4_v, E);
3299 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld4q_v, E);
3301 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst1_v, E);
3303 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst1q_v, E);
3305 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst2_v, E);
3307 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst2q_v, E);
3309 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst3_v, E);
3311 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst3q_v, E);
3313 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst4_v, E);
3315 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst4q_v, E);
3377 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld2q_lane_v, E);
3379 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld2q_lane_v, E);
3381 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld3_lane_v, E);
3383 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld3q_lane_v, E);
3385 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld4_lane_v, E);
3387 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld4q_lane_v, E);
3399 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst2_lane_v, E);
3401 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst2q_lane_v, E);
3403 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst3_lane_v, E);
3405 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst3q_lane_v, E);
3407 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst4_lane_v, E);
3409 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vst4q_lane_v, E);
3411 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld1_dup_v, E);
3413 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vld1q_dup_v, E);
3652 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vpaddl_v, E);
3655 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vpadal_v, E);
3658 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqabs_v, E);
3661 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqneg_v, E);
3667 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vabs_v, E);
3681 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcls_v, E);
3684 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vclz_v, E);
3687 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcnt_v, E);
3693 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vmovn_v, E);
3695 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqmovun_v, E);
3697 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vqmovn_v, E);
3699 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvt_f16_v, E);
3701 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvt_f32_f16, E);
3766 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvtq_u32_v, E);
3891 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrecpe_v, E);
3894 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vrsqrte_v, E);
3902 return EmitARMBuiltinExpr(ARM::BI__builtin_neon_vcvt_f32_v, E);
3928 if (BuiltinID == ARM::BI__clear_cache) {
3940 if (BuiltinID == ARM::BI__builtin_arm_ldrexd ||
3941 (BuiltinID == ARM::BI__builtin_arm_ldrex &&
3960 if (BuiltinID == ARM::BI__builtin_arm_ldrex) {
3980 if (BuiltinID == ARM::BI__builtin_arm_strexd ||
3981 (BuiltinID == ARM::BI__builtin_arm_strex &&
3999 if (BuiltinID == ARM::BI__builtin_arm_strex) {
4019 if (BuiltinID == ARM::BI__builtin_arm_clrex) {
4024 if (BuiltinID == ARM::BI__builtin_arm_sevl) {
4032 case ARM::BI__builtin_arm_crc32b:
4034 case ARM::BI__builtin_arm_crc32cb:
4036 case ARM::BI__builtin_arm_crc32h:
4038 case ARM::BI__builtin_arm_crc32ch:
4040 case ARM::BI__builtin_arm_crc32w:
4041 case ARM::BI__builtin_arm_crc32d:
4043 case ARM::BI__builtin_arm_crc32cw:
4044 case ARM::BI__builtin_arm_crc32cd:
4054 if (BuiltinID == ARM::BI__builtin_arm_crc32d ||
4055 BuiltinID == ARM::BI__builtin_arm_crc32cd) {
4077 case ARM::BI__builtin_neon_vld1_v:
4078 case ARM::BI__builtin_neon_vld1q_v:
4079 case ARM::BI__builtin_neon_vld1q_lane_v:
4080 case ARM::BI__builtin_neon_vld1_lane_v:
4081 case ARM::BI__builtin_neon_vld1_dup_v:
4082 case ARM::BI__builtin_neon_vld1q_dup_v:
4083 case ARM::BI__builtin_neon_vst1_v:
4084 case ARM::BI__builtin_neon_vst1q_v:
4085 case ARM::BI__builtin_neon_vst1q_lane_v:
4086 case ARM::BI__builtin_neon_vst1_lane_v:
4087 case ARM::BI__builtin_neon_vst2_v:
4088 case ARM::BI__builtin_neon_vst2q_v:
4089 case ARM::BI__builtin_neon_vst2_lane_v:
4090 case ARM::BI__builtin_neon_vst2q_lane_v:
4091 case ARM::BI__builtin_neon_vst3_v:
4092 case ARM::BI__builtin_neon_vst3q_v:
4093 case ARM::BI__builtin_neon_vst3_lane_v:
4094 case ARM::BI__builtin_neon_vst3q_lane_v:
4095 case ARM::BI__builtin_neon_vst4_v:
4096 case ARM::BI__builtin_neon_vst4q_v:
4097 case ARM::BI__builtin_neon_vst4_lane_v:
4098 case ARM::BI__builtin_neon_vst4q_lane_v:
4110 case ARM::BI__builtin_neon_vld2_v:
4111 case ARM::BI__builtin_neon_vld2q_v:
4112 case ARM::BI__builtin_neon_vld3_v:
4113 case ARM::BI__builtin_neon_vld3q_v:
4114 case ARM::BI__builtin_neon_vld4_v:
4115 case ARM::BI__builtin_neon_vld4q_v:
4116 case ARM::BI__builtin_neon_vld2_lane_v:
4117 case ARM::BI__builtin_neon_vld2q_lane_v:
4118 case ARM::BI__builtin_neon_vld3_lane_v:
4119 case ARM::BI__builtin_neon_vld3q_lane_v:
4120 case ARM::BI__builtin_neon_vld4_lane_v:
4121 case ARM::BI__builtin_neon_vld4q_lane_v:
4122 case ARM::BI__builtin_neon_vld2_dup_v:
4123 case ARM::BI__builtin_neon_vld3_dup_v:
4124 case ARM::BI__builtin_neon_vld4_dup_v:
4141 case ARM::BI__builtin_neon_vget_lane_i8:
4142 case ARM::BI__builtin_neon_vget_lane_i16:
4143 case ARM::BI__builtin_neon_vget_lane_i32:
4144 case ARM::BI__builtin_neon_vget_lane_i64:
4145 case ARM::BI__builtin_neon_vget_lane_f32:
4146 case ARM::BI__builtin_neon_vgetq_lane_i8:
4147 case ARM::BI__builtin_neon_vgetq_lane_i16:
4148 case ARM::BI__builtin_neon_vgetq_lane_i32:
4149 case ARM::BI__builtin_neon_vgetq_lane_i64:
4150 case ARM::BI__builtin_neon_vgetq_lane_f32:
4153 case ARM::BI__builtin_neon_vset_lane_i8:
4154 case ARM::BI__builtin_neon_vset_lane_i16:
4155 case ARM::BI__builtin_neon_vset_lane_i32:
4156 case ARM::BI__builtin_neon_vset_lane_i64:
4157 case ARM::BI__builtin_neon_vset_lane_f32:
4158 case ARM::BI__builtin_neon_vsetq_lane_i8:
4159 case ARM::BI__builtin_neon_vsetq_lane_i16:
4160 case ARM::BI__builtin_neon_vsetq_lane_i32:
4161 case ARM::BI__builtin_neon_vsetq_lane_i64:
4162 case ARM::BI__builtin_neon_vsetq_lane_f32:
4173 if (BuiltinID == ARM::BI__builtin_arm_vcvtr_f ||
4174 BuiltinID == ARM::BI__builtin_arm_vcvtr_d) {
4177 if (BuiltinID == ARM::BI__builtin_arm_vcvtr_f)
4205 case ARM::BI__builtin_neon_vbsl_v:
4206 case ARM::BI__builtin_neon_vbslq_v:
4209 case ARM::BI__builtin_neon_vabd_v:
4210 case ARM::BI__builtin_neon_vabdq_v:
4213 case ARM::BI__builtin_neon_vabs_v:
4214 case ARM::BI__builtin_neon_vabsq_v:
4217 case ARM::BI__builtin_neon_vaddhn_v: {
4235 case ARM::BI__builtin_neon_vcale_v:
4237 case ARM::BI__builtin_neon_vcage_v: {
4241 case ARM::BI__builtin_neon_vcaleq_v:
4243 case ARM::BI__builtin_neon_vcageq_v: {
4247 case ARM::BI__builtin_neon_vcalt_v:
4249 case ARM::BI__builtin_neon_vcagt_v: {
4253 case ARM::BI__builtin_neon_vcaltq_v:
4255 case ARM::BI__builtin_neon_vcagtq_v: {
4259 case ARM::BI__builtin_neon_vcls_v:
4260 case ARM::BI__builtin_neon_vclsq_v: {
4264 case ARM::BI__builtin_neon_vclz_v:
4265 case ARM::BI__builtin_neon_vclzq_v: {
4267 // for whether or not clz of zero is undefined; on ARM it isn't.
4272 case ARM::BI__builtin_neon_vcnt_v:
4273 case ARM::BI__builtin_neon_vcntq_v: {
4278 case ARM::BI__builtin_neon_vcvt_f16_v: {
4284 case ARM::BI__builtin_neon_vcvt_f32_f16: {
4290 case ARM::BI__builtin_neon_vcvt_f32_v:
4291 case ARM::BI__builtin_neon_vcvtq_f32_v:
4296 case ARM::BI__builtin_neon_vcvt_s32_v:
4297 case ARM::BI__builtin_neon_vcvt_u32_v:
4298 case ARM::BI__builtin_neon_vcvtq_s32_v:
4299 case ARM::BI__builtin_neon_vcvtq_u32_v: {
4306 case ARM::BI__builtin_neon_vcvt_n_f32_v:
4307 case ARM::BI__builtin_neon_vcvtq_n_f32_v: {
4316 case ARM::BI__builtin_neon_vcvt_n_s32_v:
4317 case ARM::BI__builtin_neon_vcvt_n_u32_v:
4318 case ARM::BI__builtin_neon_vcvtq_n_s32_v:
4319 case ARM::BI__builtin_neon_vcvtq_n_u32_v: {
4328 case ARM::BI__builtin_neon_vext_v:
4329 case ARM::BI__builtin_neon_vextq_v: {
4340 case ARM::BI__builtin_neon_vhadd_v:
4341 case ARM::BI__builtin_neon_vhaddq_v:
4344 case ARM::BI__builtin_neon_vhsub_v:
4345 case ARM::BI__builtin_neon_vhsubq_v:
4348 case ARM::BI__builtin_neon_vld1_v:
4349 case ARM::BI__builtin_neon_vld1q_v:
4353 case ARM::BI__builtin_neon_vld1q_lane_v:
4374 case ARM::BI__builtin_neon_vld1_lane_v: {
4382 case ARM::BI__builtin_neon_vld1_dup_v:
4383 case ARM::BI__builtin_neon_vld1q_dup_v: {
4393 case ARM::BI__builtin_neon_vld2_v:
4394 case ARM::BI__builtin_neon_vld2q_v: {
4401 case ARM::BI__builtin_neon_vld3_v:
4402 case ARM::BI__builtin_neon_vld3q_v: {
4409 case ARM::BI__builtin_neon_vld4_v:
4410 case ARM::BI__builtin_neon_vld4q_v: {
4417 case ARM::BI__builtin_neon_vld2_lane_v:
4418 case ARM::BI__builtin_neon_vld2q_lane_v: {
4428 case ARM::BI__builtin_neon_vld3_lane_v:
4429 case ARM::BI__builtin_neon_vld3q_lane_v: {
4440 case ARM::BI__builtin_neon_vld4_lane_v:
4441 case ARM::BI__builtin_neon_vld4q_lane_v: {
4453 case ARM::BI__builtin_neon_vld2_dup_v:
4454 case ARM::BI__builtin_neon_vld3_dup_v:
4455 case ARM::BI__builtin_neon_vld4_dup_v: {
4459 case ARM::BI__builtin_neon_vld2_dup_v:
4462 case ARM::BI__builtin_neon_vld3_dup_v:
4465 case ARM::BI__builtin_neon_vld4_dup_v:
4477 case ARM::BI__builtin_neon_vld2_dup_v:
4480 case ARM::BI__builtin_neon_vld3_dup_v:
4483 case ARM::BI__builtin_neon_vld4_dup_v:
4512 case ARM::BI__builtin_neon_vmax_v:
4513 case ARM::BI__builtin_neon_vmaxq_v:
4516 case ARM::BI__builtin_neon_vmin_v:
4517 case ARM::BI__builtin_neon_vminq_v:
4520 case ARM::BI__builtin_neon_vmovl_v: {
4527 case ARM::BI__builtin_neon_vmovn_v: {
4532 case ARM::BI__builtin_neon_vmul_v:
4533 case ARM::BI__builtin_neon_vmulq_v:
4537 case ARM::BI__builtin_neon_vmull_v:
4546 case ARM::BI__builtin_neon_vfma_v:
4547 case ARM::BI__builtin_neon_vfmaq_v: {
4556 case ARM::BI__builtin_neon_vpadal_v:
4557 case ARM::BI__builtin_neon_vpadalq_v: {
4568 case ARM::BI__builtin_neon_vpadd_v:
4571 case ARM::BI__builtin_neon_vpaddl_v:
4572 case ARM::BI__builtin_neon_vpaddlq_v: {
4582 case ARM::BI__builtin_neon_vpmax_v:
4585 case ARM::BI__builtin_neon_vpmin_v:
4588 case ARM::BI__builtin_neon_vqabs_v:
4589 case ARM::BI__builtin_neon_vqabsq_v:
4592 case ARM::BI__builtin_neon_vqadd_v:
4593 case ARM::BI__builtin_neon_vqaddq_v:
4596 case ARM::BI__builtin_neon_vqdmlal_v: {
4607 case ARM::BI__builtin_neon_vqdmlsl_v: {
4618 case ARM::BI__builtin_neon_vqdmulh_v:
4619 case ARM::BI__builtin_neon_vqdmulhq_v:
4622 case ARM::BI__builtin_neon_vqdmull_v:
4625 case ARM::BI__builtin_neon_vqmovn_v:
4628 case ARM::BI__builtin_neon_vqmovun_v:
4631 case ARM::BI__builtin_neon_vqneg_v:
4632 case ARM::BI__builtin_neon_vqnegq_v:
4635 case ARM::BI__builtin_neon_vqrdmulh_v:
4636 case ARM::BI__builtin_neon_vqrdmulhq_v:
4639 case ARM::BI__builtin_neon_vqrshl_v:
4640 case ARM::BI__builtin_neon_vqrshlq_v:
4643 case ARM::BI__builtin_neon_vqrshrn_n_v:
4648 case ARM::BI__builtin_neon_vqrshrun_n_v:
4651 case ARM::BI__builtin_neon_vqshl_v:
4652 case ARM::BI__builtin_neon_vqshlq_v:
4655 case ARM::BI__builtin_neon_vqshl_n_v:
4656 case ARM::BI__builtin_neon_vqshlq_n_v:
4660 case ARM::BI__builtin_neon_vqshlu_n_v:
4661 case ARM::BI__builtin_neon_vqshluq_n_v:
4664 case ARM::BI__builtin_neon_vqshrn_n_v:
4668 case ARM::BI__builtin_neon_vqshrun_n_v:
4671 case ARM::BI__builtin_neon_vqsub_v:
4672 case ARM::BI__builtin_neon_vqsubq_v:
4675 case ARM::BI__builtin_neon_vraddhn_v:
4678 case ARM::BI__builtin_neon_vrecpe_v:
4679 case ARM::BI__builtin_neon_vrecpeq_v:
4682 case ARM::BI__builtin_neon_vrecps_v:
4683 case ARM::BI__builtin_neon_vrecpsq_v:
4686 case ARM::BI__builtin_neon_vrhadd_v:
4687 case ARM::BI__builtin_neon_vrhaddq_v:
4690 case ARM::BI__builtin_neon_vrshl_v:
4691 case ARM::BI__builtin_neon_vrshlq_v:
4694 case ARM::BI__builtin_neon_vrshrn_n_v:
4697 case ARM::BI__builtin_neon_vrshr_n_v:
4698 case ARM::BI__builtin_neon_vrshrq_n_v:
4701 case ARM::BI__builtin_neon_vrsqrte_v:
4702 case ARM::BI__builtin_neon_vrsqrteq_v:
4705 case ARM::BI__builtin_neon_vrsqrts_v:
4706 case ARM::BI__builtin_neon_vrsqrtsq_v:
4709 case ARM::BI__builtin_neon_vrsra_n_v:
4710 case ARM::BI__builtin_neon_vrsraq_n_v:
4717 case ARM::BI__builtin_neon_vrsubhn_v:
4720 case ARM::BI__builtin_neon_vshl_v:
4721 case ARM::BI__builtin_neon_vshlq_v:
4724 case ARM::BI__builtin_neon_vshll_n_v:
4727 case ARM::BI__builtin_neon_vshl_n_v:
4728 case ARM::BI__builtin_neon_vshlq_n_v:
4732 case ARM::BI__builtin_neon_vshrn_n_v:
4735 case ARM::BI__builtin_neon_vshr_n_v:
4736 case ARM::BI__builtin_neon_vshrq_n_v:
4738 case ARM::BI__builtin_neon_vsri_n_v:
4739 case ARM::BI__builtin_neon_vsriq_n_v:
4741 case ARM::BI__builtin_neon_vsli_n_v:
4742 case ARM::BI__builtin_neon_vsliq_n_v:
4746 case ARM::BI__builtin_neon_vsra_n_v:
4747 case ARM::BI__builtin_neon_vsraq_n_v:
4751 case ARM::BI__builtin_neon_vst1_v:
4752 case ARM::BI__builtin_neon_vst1q_v:
4756 case ARM::BI__builtin_neon_vst1q_lane_v:
4768 case ARM::BI__builtin_neon_vst1_lane_v: {
4777 case ARM::BI__builtin_neon_vst2_v:
4778 case ARM::BI__builtin_neon_vst2q_v:
4782 case ARM::BI__builtin_neon_vst2_lane_v:
4783 case ARM::BI__builtin_neon_vst2q_lane_v:
4787 case ARM::BI__builtin_neon_vst3_v:
4788 case ARM::BI__builtin_neon_vst3q_v:
4792 case ARM::BI__builtin_neon_vst3_lane_v:
4793 case ARM::BI__builtin_neon_vst3q_lane_v:
4797 case ARM::BI__builtin_neon_vst4_v:
4798 case ARM::BI__builtin_neon_vst4q_v:
4802 case ARM::BI__builtin_neon_vst4_lane_v:
4803 case ARM::BI__builtin_neon_vst4q_lane_v:
4807 case ARM::BI__builtin_neon_vsubhn_v: {
4825 case ARM::BI__builtin_neon_vtbl1_v:
4828 case ARM::BI__builtin_neon_vtbl2_v:
4831 case ARM::BI__builtin_neon_vtbl3_v:
4834 case ARM::BI__builtin_neon_vtbl4_v:
4837 case ARM::BI__builtin_neon_vtbx1_v:
4840 case ARM::BI__builtin_neon_vtbx2_v:
4843 case ARM::BI__builtin_neon_vtbx3_v:
4846 case ARM::BI__builtin_neon_vtbx4_v:
4849 case ARM::BI__builtin_neon_vtst_v:
4850 case ARM::BI__builtin_neon_vtstq_v: {
4858 case ARM::BI__builtin_neon_vtrn_v:
4859 case ARM::BI__builtin_neon_vtrnq_v: {
4878 case ARM::BI__builtin_neon_vuzp_v:
4879 case ARM::BI__builtin_neon_vuzpq_v: {
4897 case ARM::BI__builtin_neon_vzip_v:
4898 case ARM::BI__builtin_neon_vzipq_v: {