reference, declarationdefinition
definition → references, declarations, derived classes, virtual overrides
reference to multiple definitions → definitions
unreferenced

References

tools/clang/lib/CodeGen/CGBuiltin.cpp
 4447   NEONMAP1(vabs_v, arm_neon_vabs, 0),
 4448   NEONMAP1(vabsq_v, arm_neon_vabs, 0),
 4450   NEONMAP1(vaesdq_v, arm_neon_aesd, 0),
 4451   NEONMAP1(vaeseq_v, arm_neon_aese, 0),
 4452   NEONMAP1(vaesimcq_v, arm_neon_aesimc, 0),
 4453   NEONMAP1(vaesmcq_v, arm_neon_aesmc, 0),
 4454   NEONMAP1(vbsl_v, arm_neon_vbsl, AddRetType),
 4455   NEONMAP1(vbslq_v, arm_neon_vbsl, AddRetType),
 4456   NEONMAP1(vcage_v, arm_neon_vacge, 0),
 4457   NEONMAP1(vcageq_v, arm_neon_vacge, 0),
 4458   NEONMAP1(vcagt_v, arm_neon_vacgt, 0),
 4459   NEONMAP1(vcagtq_v, arm_neon_vacgt, 0),
 4460   NEONMAP1(vcale_v, arm_neon_vacge, 0),
 4461   NEONMAP1(vcaleq_v, arm_neon_vacge, 0),
 4462   NEONMAP1(vcalt_v, arm_neon_vacgt, 0),
 4463   NEONMAP1(vcaltq_v, arm_neon_vacgt, 0),
 4472   NEONMAP1(vcls_v, arm_neon_vcls, Add1ArgType),
 4473   NEONMAP1(vclsq_v, arm_neon_vcls, Add1ArgType),
 4476   NEONMAP1(vclz_v, ctlz, Add1ArgType),
 4477   NEONMAP1(vclzq_v, ctlz, Add1ArgType),
 4478   NEONMAP1(vcnt_v, ctpop, Add1ArgType),
 4479   NEONMAP1(vcntq_v, ctpop, Add1ArgType),
 4480   NEONMAP1(vcvt_f16_f32, arm_neon_vcvtfp2hf, 0),
 4482   NEONMAP1(vcvt_f32_f16, arm_neon_vcvthf2fp, 0),
 4486   NEONMAP1(vcvt_n_s16_v, arm_neon_vcvtfp2fxs, 0),
 4487   NEONMAP1(vcvt_n_s32_v, arm_neon_vcvtfp2fxs, 0),
 4488   NEONMAP1(vcvt_n_s64_v, arm_neon_vcvtfp2fxs, 0),
 4489   NEONMAP1(vcvt_n_u16_v, arm_neon_vcvtfp2fxu, 0),
 4490   NEONMAP1(vcvt_n_u32_v, arm_neon_vcvtfp2fxu, 0),
 4491   NEONMAP1(vcvt_n_u64_v, arm_neon_vcvtfp2fxu, 0),
 4498   NEONMAP1(vcvta_s16_v, arm_neon_vcvtas, 0),
 4499   NEONMAP1(vcvta_s32_v, arm_neon_vcvtas, 0),
 4500   NEONMAP1(vcvta_s64_v, arm_neon_vcvtas, 0),
 4501   NEONMAP1(vcvta_u16_v, arm_neon_vcvtau, 0),
 4502   NEONMAP1(vcvta_u32_v, arm_neon_vcvtau, 0),
 4503   NEONMAP1(vcvta_u64_v, arm_neon_vcvtau, 0),
 4504   NEONMAP1(vcvtaq_s16_v, arm_neon_vcvtas, 0),
 4505   NEONMAP1(vcvtaq_s32_v, arm_neon_vcvtas, 0),
 4506   NEONMAP1(vcvtaq_s64_v, arm_neon_vcvtas, 0),
 4507   NEONMAP1(vcvtaq_u16_v, arm_neon_vcvtau, 0),
 4508   NEONMAP1(vcvtaq_u32_v, arm_neon_vcvtau, 0),
 4509   NEONMAP1(vcvtaq_u64_v, arm_neon_vcvtau, 0),
 4510   NEONMAP1(vcvtm_s16_v, arm_neon_vcvtms, 0),
 4511   NEONMAP1(vcvtm_s32_v, arm_neon_vcvtms, 0),
 4512   NEONMAP1(vcvtm_s64_v, arm_neon_vcvtms, 0),
 4513   NEONMAP1(vcvtm_u16_v, arm_neon_vcvtmu, 0),
 4514   NEONMAP1(vcvtm_u32_v, arm_neon_vcvtmu, 0),
 4515   NEONMAP1(vcvtm_u64_v, arm_neon_vcvtmu, 0),
 4516   NEONMAP1(vcvtmq_s16_v, arm_neon_vcvtms, 0),
 4517   NEONMAP1(vcvtmq_s32_v, arm_neon_vcvtms, 0),
 4518   NEONMAP1(vcvtmq_s64_v, arm_neon_vcvtms, 0),
 4519   NEONMAP1(vcvtmq_u16_v, arm_neon_vcvtmu, 0),
 4520   NEONMAP1(vcvtmq_u32_v, arm_neon_vcvtmu, 0),
 4521   NEONMAP1(vcvtmq_u64_v, arm_neon_vcvtmu, 0),
 4522   NEONMAP1(vcvtn_s16_v, arm_neon_vcvtns, 0),
 4523   NEONMAP1(vcvtn_s32_v, arm_neon_vcvtns, 0),
 4524   NEONMAP1(vcvtn_s64_v, arm_neon_vcvtns, 0),
 4525   NEONMAP1(vcvtn_u16_v, arm_neon_vcvtnu, 0),
 4526   NEONMAP1(vcvtn_u32_v, arm_neon_vcvtnu, 0),
 4527   NEONMAP1(vcvtn_u64_v, arm_neon_vcvtnu, 0),
 4528   NEONMAP1(vcvtnq_s16_v, arm_neon_vcvtns, 0),
 4529   NEONMAP1(vcvtnq_s32_v, arm_neon_vcvtns, 0),
 4530   NEONMAP1(vcvtnq_s64_v, arm_neon_vcvtns, 0),
 4531   NEONMAP1(vcvtnq_u16_v, arm_neon_vcvtnu, 0),
 4532   NEONMAP1(vcvtnq_u32_v, arm_neon_vcvtnu, 0),
 4533   NEONMAP1(vcvtnq_u64_v, arm_neon_vcvtnu, 0),
 4534   NEONMAP1(vcvtp_s16_v, arm_neon_vcvtps, 0),
 4535   NEONMAP1(vcvtp_s32_v, arm_neon_vcvtps, 0),
 4536   NEONMAP1(vcvtp_s64_v, arm_neon_vcvtps, 0),
 4537   NEONMAP1(vcvtp_u16_v, arm_neon_vcvtpu, 0),
 4538   NEONMAP1(vcvtp_u32_v, arm_neon_vcvtpu, 0),
 4539   NEONMAP1(vcvtp_u64_v, arm_neon_vcvtpu, 0),
 4540   NEONMAP1(vcvtpq_s16_v, arm_neon_vcvtps, 0),
 4541   NEONMAP1(vcvtpq_s32_v, arm_neon_vcvtps, 0),
 4542   NEONMAP1(vcvtpq_s64_v, arm_neon_vcvtps, 0),
 4543   NEONMAP1(vcvtpq_u16_v, arm_neon_vcvtpu, 0),
 4544   NEONMAP1(vcvtpq_u32_v, arm_neon_vcvtpu, 0),
 4545   NEONMAP1(vcvtpq_u64_v, arm_neon_vcvtpu, 0),
 4550   NEONMAP1(vcvtq_n_s16_v, arm_neon_vcvtfp2fxs, 0),
 4551   NEONMAP1(vcvtq_n_s32_v, arm_neon_vcvtfp2fxs, 0),
 4552   NEONMAP1(vcvtq_n_s64_v, arm_neon_vcvtfp2fxs, 0),
 4553   NEONMAP1(vcvtq_n_u16_v, arm_neon_vcvtfp2fxu, 0),
 4554   NEONMAP1(vcvtq_n_u32_v, arm_neon_vcvtfp2fxu, 0),
 4555   NEONMAP1(vcvtq_n_u64_v, arm_neon_vcvtfp2fxu, 0),
 4573   NEONMAP1(vld1_v, arm_neon_vld1, 0),
 4574   NEONMAP1(vld1_x2_v, arm_neon_vld1x2, 0),
 4575   NEONMAP1(vld1_x3_v, arm_neon_vld1x3, 0),
 4576   NEONMAP1(vld1_x4_v, arm_neon_vld1x4, 0),
 4578   NEONMAP1(vld1q_v, arm_neon_vld1, 0),
 4579   NEONMAP1(vld1q_x2_v, arm_neon_vld1x2, 0),
 4580   NEONMAP1(vld1q_x3_v, arm_neon_vld1x3, 0),
 4581   NEONMAP1(vld1q_x4_v, arm_neon_vld1x4, 0),
 4582   NEONMAP1(vld2_dup_v, arm_neon_vld2dup, 0),
 4583   NEONMAP1(vld2_lane_v, arm_neon_vld2lane, 0),
 4584   NEONMAP1(vld2_v, arm_neon_vld2, 0),
 4585   NEONMAP1(vld2q_dup_v, arm_neon_vld2dup, 0),
 4586   NEONMAP1(vld2q_lane_v, arm_neon_vld2lane, 0),
 4587   NEONMAP1(vld2q_v, arm_neon_vld2, 0),
 4588   NEONMAP1(vld3_dup_v, arm_neon_vld3dup, 0),
 4589   NEONMAP1(vld3_lane_v, arm_neon_vld3lane, 0),
 4590   NEONMAP1(vld3_v, arm_neon_vld3, 0),
 4591   NEONMAP1(vld3q_dup_v, arm_neon_vld3dup, 0),
 4592   NEONMAP1(vld3q_lane_v, arm_neon_vld3lane, 0),
 4593   NEONMAP1(vld3q_v, arm_neon_vld3, 0),
 4594   NEONMAP1(vld4_dup_v, arm_neon_vld4dup, 0),
 4595   NEONMAP1(vld4_lane_v, arm_neon_vld4lane, 0),
 4596   NEONMAP1(vld4_v, arm_neon_vld4, 0),
 4597   NEONMAP1(vld4q_dup_v, arm_neon_vld4dup, 0),
 4598   NEONMAP1(vld4q_lane_v, arm_neon_vld4lane, 0),
 4599   NEONMAP1(vld4q_v, arm_neon_vld4, 0),
 4601   NEONMAP1(vmaxnm_v, arm_neon_vmaxnm, Add1ArgType),
 4602   NEONMAP1(vmaxnmq_v, arm_neon_vmaxnm, Add1ArgType),
 4605   NEONMAP1(vminnm_v, arm_neon_vminnm, Add1ArgType),
 4606   NEONMAP1(vminnmq_v, arm_neon_vminnm, Add1ArgType),
 4610   NEONMAP1(vmul_v, arm_neon_vmulp, Add1ArgType),
 4612   NEONMAP1(vmulq_v, arm_neon_vmulp, Add1ArgType),
 4615   NEONMAP1(vpadd_v, arm_neon_vpadd, Add1ArgType),
 4618   NEONMAP1(vpaddq_v, arm_neon_vpadd, Add1ArgType),
 4621   NEONMAP1(vqabs_v, arm_neon_vqabs, Add1ArgType),
 4622   NEONMAP1(vqabsq_v, arm_neon_vqabs, Add1ArgType),
 4627   NEONMAP1(vqdmulh_v, arm_neon_vqdmulh, Add1ArgType),
 4628   NEONMAP1(vqdmulhq_v, arm_neon_vqdmulh, Add1ArgType),
 4629   NEONMAP1(vqdmull_v, arm_neon_vqdmull, Add1ArgType),
 4631   NEONMAP1(vqmovun_v, arm_neon_vqmovnsu, Add1ArgType),
 4632   NEONMAP1(vqneg_v, arm_neon_vqneg, Add1ArgType),
 4633   NEONMAP1(vqnegq_v, arm_neon_vqneg, Add1ArgType),
 4634   NEONMAP1(vqrdmulh_v, arm_neon_vqrdmulh, Add1ArgType),
 4635   NEONMAP1(vqrdmulhq_v, arm_neon_vqrdmulh, Add1ArgType),
 4642   NEONMAP1(vqshlu_n_v, arm_neon_vqshiftsu, 0),
 4643   NEONMAP1(vqshluq_n_v, arm_neon_vqshiftsu, 0),
 4646   NEONMAP1(vraddhn_v, arm_neon_vraddhn, Add1ArgType),
 4649   NEONMAP1(vrecps_v, arm_neon_vrecps, Add1ArgType),
 4650   NEONMAP1(vrecpsq_v, arm_neon_vrecps, Add1ArgType),
 4653   NEONMAP1(vrnd_v, arm_neon_vrintz, Add1ArgType),
 4654   NEONMAP1(vrnda_v, arm_neon_vrinta, Add1ArgType),
 4655   NEONMAP1(vrndaq_v, arm_neon_vrinta, Add1ArgType),
 4658   NEONMAP1(vrndm_v, arm_neon_vrintm, Add1ArgType),
 4659   NEONMAP1(vrndmq_v, arm_neon_vrintm, Add1ArgType),
 4660   NEONMAP1(vrndn_v, arm_neon_vrintn, Add1ArgType),
 4661   NEONMAP1(vrndnq_v, arm_neon_vrintn, Add1ArgType),
 4662   NEONMAP1(vrndp_v, arm_neon_vrintp, Add1ArgType),
 4663   NEONMAP1(vrndpq_v, arm_neon_vrintp, Add1ArgType),
 4664   NEONMAP1(vrndq_v, arm_neon_vrintz, Add1ArgType),
 4665   NEONMAP1(vrndx_v, arm_neon_vrintx, Add1ArgType),
 4666   NEONMAP1(vrndxq_v, arm_neon_vrintx, Add1ArgType),
 4673   NEONMAP1(vrsqrts_v, arm_neon_vrsqrts, Add1ArgType),
 4674   NEONMAP1(vrsqrtsq_v, arm_neon_vrsqrts, Add1ArgType),
 4675   NEONMAP1(vrsubhn_v, arm_neon_vrsubhn, Add1ArgType),
 4676   NEONMAP1(vsha1su0q_v, arm_neon_sha1su0, 0),
 4677   NEONMAP1(vsha1su1q_v, arm_neon_sha1su1, 0),
 4678   NEONMAP1(vsha256h2q_v, arm_neon_sha256h2, 0),
 4679   NEONMAP1(vsha256hq_v, arm_neon_sha256h, 0),
 4680   NEONMAP1(vsha256su0q_v, arm_neon_sha256su0, 0),
 4681   NEONMAP1(vsha256su1q_v, arm_neon_sha256su1, 0),
 4690   NEONMAP1(vst1_v, arm_neon_vst1, 0),
 4691   NEONMAP1(vst1_x2_v, arm_neon_vst1x2, 0),
 4692   NEONMAP1(vst1_x3_v, arm_neon_vst1x3, 0),
 4693   NEONMAP1(vst1_x4_v, arm_neon_vst1x4, 0),
 4694   NEONMAP1(vst1q_v, arm_neon_vst1, 0),
 4695   NEONMAP1(vst1q_x2_v, arm_neon_vst1x2, 0),
 4696   NEONMAP1(vst1q_x3_v, arm_neon_vst1x3, 0),
 4697   NEONMAP1(vst1q_x4_v, arm_neon_vst1x4, 0),
 4698   NEONMAP1(vst2_lane_v, arm_neon_vst2lane, 0),
 4699   NEONMAP1(vst2_v, arm_neon_vst2, 0),
 4700   NEONMAP1(vst2q_lane_v, arm_neon_vst2lane, 0),
 4701   NEONMAP1(vst2q_v, arm_neon_vst2, 0),
 4702   NEONMAP1(vst3_lane_v, arm_neon_vst3lane, 0),
 4703   NEONMAP1(vst3_v, arm_neon_vst3, 0),
 4704   NEONMAP1(vst3q_lane_v, arm_neon_vst3lane, 0),
 4705   NEONMAP1(vst3q_v, arm_neon_vst3, 0),
 4706   NEONMAP1(vst4_lane_v, arm_neon_vst4lane, 0),
 4707   NEONMAP1(vst4_v, arm_neon_vst4, 0),
 4708   NEONMAP1(vst4q_lane_v, arm_neon_vst4lane, 0),
 4709   NEONMAP1(vst4q_v, arm_neon_vst4, 0),
 4722   NEONMAP1(vabs_v, aarch64_neon_abs, 0),
 4723   NEONMAP1(vabsq_v, aarch64_neon_abs, 0),
 4725   NEONMAP1(vaesdq_v, aarch64_crypto_aesd, 0),
 4726   NEONMAP1(vaeseq_v, aarch64_crypto_aese, 0),
 4727   NEONMAP1(vaesimcq_v, aarch64_crypto_aesimc, 0),
 4728   NEONMAP1(vaesmcq_v, aarch64_crypto_aesmc, 0),
 4729   NEONMAP1(vcage_v, aarch64_neon_facge, 0),
 4730   NEONMAP1(vcageq_v, aarch64_neon_facge, 0),
 4731   NEONMAP1(vcagt_v, aarch64_neon_facgt, 0),
 4732   NEONMAP1(vcagtq_v, aarch64_neon_facgt, 0),
 4733   NEONMAP1(vcale_v, aarch64_neon_facge, 0),
 4734   NEONMAP1(vcaleq_v, aarch64_neon_facge, 0),
 4735   NEONMAP1(vcalt_v, aarch64_neon_facgt, 0),
 4736   NEONMAP1(vcaltq_v, aarch64_neon_facgt, 0),
 4745   NEONMAP1(vcls_v, aarch64_neon_cls, Add1ArgType),
 4746   NEONMAP1(vclsq_v, aarch64_neon_cls, Add1ArgType),
 4749   NEONMAP1(vclz_v, ctlz, Add1ArgType),
 4750   NEONMAP1(vclzq_v, ctlz, Add1ArgType),
 4751   NEONMAP1(vcnt_v, ctpop, Add1ArgType),
 4752   NEONMAP1(vcntq_v, ctpop, Add1ArgType),
 4753   NEONMAP1(vcvt_f16_f32, aarch64_neon_vcvtfp2hf, 0),
 4755   NEONMAP1(vcvt_f32_f16, aarch64_neon_vcvthf2fp, 0),
 4760   NEONMAP1(vcvt_n_s16_v, aarch64_neon_vcvtfp2fxs, 0),
 4761   NEONMAP1(vcvt_n_s32_v, aarch64_neon_vcvtfp2fxs, 0),
 4762   NEONMAP1(vcvt_n_s64_v, aarch64_neon_vcvtfp2fxs, 0),
 4763   NEONMAP1(vcvt_n_u16_v, aarch64_neon_vcvtfp2fxu, 0),
 4764   NEONMAP1(vcvt_n_u32_v, aarch64_neon_vcvtfp2fxu, 0),
 4765   NEONMAP1(vcvt_n_u64_v, aarch64_neon_vcvtfp2fxu, 0),
 4771   NEONMAP1(vcvtq_n_s16_v, aarch64_neon_vcvtfp2fxs, 0),
 4772   NEONMAP1(vcvtq_n_s32_v, aarch64_neon_vcvtfp2fxs, 0),
 4773   NEONMAP1(vcvtq_n_s64_v, aarch64_neon_vcvtfp2fxs, 0),
 4774   NEONMAP1(vcvtq_n_u16_v, aarch64_neon_vcvtfp2fxu, 0),
 4775   NEONMAP1(vcvtq_n_u32_v, aarch64_neon_vcvtfp2fxu, 0),
 4776   NEONMAP1(vcvtq_n_u64_v, aarch64_neon_vcvtfp2fxu, 0),
 4777   NEONMAP1(vcvtx_f32_v, aarch64_neon_fcvtxn, AddRetType | Add1ArgType),
 4784   NEONMAP1(vfmlal_high_v, aarch64_neon_fmlal2, 0),
 4785   NEONMAP1(vfmlal_low_v, aarch64_neon_fmlal, 0),
 4786   NEONMAP1(vfmlalq_high_v, aarch64_neon_fmlal2, 0),
 4787   NEONMAP1(vfmlalq_low_v, aarch64_neon_fmlal, 0),
 4788   NEONMAP1(vfmlsl_high_v, aarch64_neon_fmlsl2, 0),
 4789   NEONMAP1(vfmlsl_low_v, aarch64_neon_fmlsl, 0),
 4790   NEONMAP1(vfmlslq_high_v, aarch64_neon_fmlsl2, 0),
 4791   NEONMAP1(vfmlslq_low_v, aarch64_neon_fmlsl, 0),
 4796   NEONMAP1(vld1_x2_v, aarch64_neon_ld1x2, 0),
 4797   NEONMAP1(vld1_x3_v, aarch64_neon_ld1x3, 0),
 4798   NEONMAP1(vld1_x4_v, aarch64_neon_ld1x4, 0),
 4799   NEONMAP1(vld1q_x2_v, aarch64_neon_ld1x2, 0),
 4800   NEONMAP1(vld1q_x3_v, aarch64_neon_ld1x3, 0),
 4801   NEONMAP1(vld1q_x4_v, aarch64_neon_ld1x4, 0),
 4804   NEONMAP1(vmul_v, aarch64_neon_pmul, Add1ArgType),
 4805   NEONMAP1(vmulq_v, aarch64_neon_pmul, Add1ArgType),
 4806   NEONMAP1(vpadd_v, aarch64_neon_addp, Add1ArgType),
 4809   NEONMAP1(vpaddq_v, aarch64_neon_addp, Add1ArgType),
 4810   NEONMAP1(vqabs_v, aarch64_neon_sqabs, Add1ArgType),
 4811   NEONMAP1(vqabsq_v, aarch64_neon_sqabs, Add1ArgType),
 4816   NEONMAP1(vqdmulh_v, aarch64_neon_sqdmulh, Add1ArgType),
 4817   NEONMAP1(vqdmulhq_v, aarch64_neon_sqdmulh, Add1ArgType),
 4818   NEONMAP1(vqdmull_v, aarch64_neon_sqdmull, Add1ArgType),
 4820   NEONMAP1(vqmovun_v, aarch64_neon_sqxtun, Add1ArgType),
 4821   NEONMAP1(vqneg_v, aarch64_neon_sqneg, Add1ArgType),
 4822   NEONMAP1(vqnegq_v, aarch64_neon_sqneg, Add1ArgType),
 4823   NEONMAP1(vqrdmulh_v, aarch64_neon_sqrdmulh, Add1ArgType),
 4824   NEONMAP1(vqrdmulhq_v, aarch64_neon_sqrdmulh, Add1ArgType),
 4831   NEONMAP1(vqshlu_n_v, aarch64_neon_sqshlu, 0),
 4832   NEONMAP1(vqshluq_n_v, aarch64_neon_sqshlu, 0),
 4835   NEONMAP1(vraddhn_v, aarch64_neon_raddhn, Add1ArgType),
 4838   NEONMAP1(vrecps_v, aarch64_neon_frecps, Add1ArgType),
 4839   NEONMAP1(vrecpsq_v, aarch64_neon_frecps, Add1ArgType),
 4850   NEONMAP1(vrsqrts_v, aarch64_neon_frsqrts, Add1ArgType),
 4851   NEONMAP1(vrsqrtsq_v, aarch64_neon_frsqrts, Add1ArgType),
 4852   NEONMAP1(vrsubhn_v, aarch64_neon_rsubhn, Add1ArgType),
 4853   NEONMAP1(vsha1su0q_v, aarch64_crypto_sha1su0, 0),
 4854   NEONMAP1(vsha1su1q_v, aarch64_crypto_sha1su1, 0),
 4855   NEONMAP1(vsha256h2q_v, aarch64_crypto_sha256h2, 0),
 4856   NEONMAP1(vsha256hq_v, aarch64_crypto_sha256h, 0),
 4857   NEONMAP1(vsha256su0q_v, aarch64_crypto_sha256su0, 0),
 4858   NEONMAP1(vsha256su1q_v, aarch64_crypto_sha256su1, 0),
 4867   NEONMAP1(vst1_x2_v, aarch64_neon_st1x2, 0),
 4868   NEONMAP1(vst1_x3_v, aarch64_neon_st1x3, 0),
 4869   NEONMAP1(vst1_x4_v, aarch64_neon_st1x4, 0),
 4870   NEONMAP1(vst1q_x2_v, aarch64_neon_st1x2, 0),
 4871   NEONMAP1(vst1q_x3_v, aarch64_neon_st1x3, 0),
 4872   NEONMAP1(vst1q_x4_v, aarch64_neon_st1x4, 0),
 4879   NEONMAP1(vabdd_f64, aarch64_sisd_fabd, Add1ArgType),
 4880   NEONMAP1(vabds_f32, aarch64_sisd_fabd, Add1ArgType),
 4881   NEONMAP1(vabsd_s64, aarch64_neon_abs, Add1ArgType),
 4882   NEONMAP1(vaddlv_s32, aarch64_neon_saddlv, AddRetType | Add1ArgType),
 4883   NEONMAP1(vaddlv_u32, aarch64_neon_uaddlv, AddRetType | Add1ArgType),
 4884   NEONMAP1(vaddlvq_s32, aarch64_neon_saddlv, AddRetType | Add1ArgType),
 4885   NEONMAP1(vaddlvq_u32, aarch64_neon_uaddlv, AddRetType | Add1ArgType),
 4886   NEONMAP1(vaddv_f32, aarch64_neon_faddv, AddRetType | Add1ArgType),
 4887   NEONMAP1(vaddv_s32, aarch64_neon_saddv, AddRetType | Add1ArgType),
 4888   NEONMAP1(vaddv_u32, aarch64_neon_uaddv, AddRetType | Add1ArgType),
 4889   NEONMAP1(vaddvq_f32, aarch64_neon_faddv, AddRetType | Add1ArgType),
 4890   NEONMAP1(vaddvq_f64, aarch64_neon_faddv, AddRetType | Add1ArgType),
 4891   NEONMAP1(vaddvq_s32, aarch64_neon_saddv, AddRetType | Add1ArgType),
 4892   NEONMAP1(vaddvq_s64, aarch64_neon_saddv, AddRetType | Add1ArgType),
 4893   NEONMAP1(vaddvq_u32, aarch64_neon_uaddv, AddRetType | Add1ArgType),
 4894   NEONMAP1(vaddvq_u64, aarch64_neon_uaddv, AddRetType | Add1ArgType),
 4895   NEONMAP1(vcaged_f64, aarch64_neon_facge, AddRetType | Add1ArgType),
 4896   NEONMAP1(vcages_f32, aarch64_neon_facge, AddRetType | Add1ArgType),
 4897   NEONMAP1(vcagtd_f64, aarch64_neon_facgt, AddRetType | Add1ArgType),
 4898   NEONMAP1(vcagts_f32, aarch64_neon_facgt, AddRetType | Add1ArgType),
 4899   NEONMAP1(vcaled_f64, aarch64_neon_facge, AddRetType | Add1ArgType),
 4900   NEONMAP1(vcales_f32, aarch64_neon_facge, AddRetType | Add1ArgType),
 4901   NEONMAP1(vcaltd_f64, aarch64_neon_facgt, AddRetType | Add1ArgType),
 4902   NEONMAP1(vcalts_f32, aarch64_neon_facgt, AddRetType | Add1ArgType),
 4903   NEONMAP1(vcvtad_s64_f64, aarch64_neon_fcvtas, AddRetType | Add1ArgType),
 4904   NEONMAP1(vcvtad_u64_f64, aarch64_neon_fcvtau, AddRetType | Add1ArgType),
 4905   NEONMAP1(vcvtas_s32_f32, aarch64_neon_fcvtas, AddRetType | Add1ArgType),
 4906   NEONMAP1(vcvtas_u32_f32, aarch64_neon_fcvtau, AddRetType | Add1ArgType),
 4907   NEONMAP1(vcvtd_n_f64_s64, aarch64_neon_vcvtfxs2fp, AddRetType | Add1ArgType),
 4908   NEONMAP1(vcvtd_n_f64_u64, aarch64_neon_vcvtfxu2fp, AddRetType | Add1ArgType),
 4909   NEONMAP1(vcvtd_n_s64_f64, aarch64_neon_vcvtfp2fxs, AddRetType | Add1ArgType),
 4910   NEONMAP1(vcvtd_n_u64_f64, aarch64_neon_vcvtfp2fxu, AddRetType | Add1ArgType),
 4911   NEONMAP1(vcvtmd_s64_f64, aarch64_neon_fcvtms, AddRetType | Add1ArgType),
 4912   NEONMAP1(vcvtmd_u64_f64, aarch64_neon_fcvtmu, AddRetType | Add1ArgType),
 4913   NEONMAP1(vcvtms_s32_f32, aarch64_neon_fcvtms, AddRetType | Add1ArgType),
 4914   NEONMAP1(vcvtms_u32_f32, aarch64_neon_fcvtmu, AddRetType | Add1ArgType),
 4915   NEONMAP1(vcvtnd_s64_f64, aarch64_neon_fcvtns, AddRetType | Add1ArgType),
 4916   NEONMAP1(vcvtnd_u64_f64, aarch64_neon_fcvtnu, AddRetType | Add1ArgType),
 4917   NEONMAP1(vcvtns_s32_f32, aarch64_neon_fcvtns, AddRetType | Add1ArgType),
 4918   NEONMAP1(vcvtns_u32_f32, aarch64_neon_fcvtnu, AddRetType | Add1ArgType),
 4919   NEONMAP1(vcvtpd_s64_f64, aarch64_neon_fcvtps, AddRetType | Add1ArgType),
 4920   NEONMAP1(vcvtpd_u64_f64, aarch64_neon_fcvtpu, AddRetType | Add1ArgType),
 4921   NEONMAP1(vcvtps_s32_f32, aarch64_neon_fcvtps, AddRetType | Add1ArgType),
 4922   NEONMAP1(vcvtps_u32_f32, aarch64_neon_fcvtpu, AddRetType | Add1ArgType),
 4923   NEONMAP1(vcvts_n_f32_s32, aarch64_neon_vcvtfxs2fp, AddRetType | Add1ArgType),
 4924   NEONMAP1(vcvts_n_f32_u32, aarch64_neon_vcvtfxu2fp, AddRetType | Add1ArgType),
 4925   NEONMAP1(vcvts_n_s32_f32, aarch64_neon_vcvtfp2fxs, AddRetType | Add1ArgType),
 4926   NEONMAP1(vcvts_n_u32_f32, aarch64_neon_vcvtfp2fxu, AddRetType | Add1ArgType),
 4927   NEONMAP1(vcvtxd_f32_f64, aarch64_sisd_fcvtxn, 0),
 4928   NEONMAP1(vmaxnmv_f32, aarch64_neon_fmaxnmv, AddRetType | Add1ArgType),
 4929   NEONMAP1(vmaxnmvq_f32, aarch64_neon_fmaxnmv, AddRetType | Add1ArgType),
 4930   NEONMAP1(vmaxnmvq_f64, aarch64_neon_fmaxnmv, AddRetType | Add1ArgType),
 4931   NEONMAP1(vmaxv_f32, aarch64_neon_fmaxv, AddRetType | Add1ArgType),
 4932   NEONMAP1(vmaxv_s32, aarch64_neon_smaxv, AddRetType | Add1ArgType),
 4933   NEONMAP1(vmaxv_u32, aarch64_neon_umaxv, AddRetType | Add1ArgType),
 4934   NEONMAP1(vmaxvq_f32, aarch64_neon_fmaxv, AddRetType | Add1ArgType),
 4935   NEONMAP1(vmaxvq_f64, aarch64_neon_fmaxv, AddRetType | Add1ArgType),
 4936   NEONMAP1(vmaxvq_s32, aarch64_neon_smaxv, AddRetType | Add1ArgType),
 4937   NEONMAP1(vmaxvq_u32, aarch64_neon_umaxv, AddRetType | Add1ArgType),
 4938   NEONMAP1(vminnmv_f32, aarch64_neon_fminnmv, AddRetType | Add1ArgType),
 4939   NEONMAP1(vminnmvq_f32, aarch64_neon_fminnmv, AddRetType | Add1ArgType),
 4940   NEONMAP1(vminnmvq_f64, aarch64_neon_fminnmv, AddRetType | Add1ArgType),
 4941   NEONMAP1(vminv_f32, aarch64_neon_fminv, AddRetType | Add1ArgType),
 4942   NEONMAP1(vminv_s32, aarch64_neon_sminv, AddRetType | Add1ArgType),
 4943   NEONMAP1(vminv_u32, aarch64_neon_uminv, AddRetType | Add1ArgType),
 4944   NEONMAP1(vminvq_f32, aarch64_neon_fminv, AddRetType | Add1ArgType),
 4945   NEONMAP1(vminvq_f64, aarch64_neon_fminv, AddRetType | Add1ArgType),
 4946   NEONMAP1(vminvq_s32, aarch64_neon_sminv, AddRetType | Add1ArgType),
 4947   NEONMAP1(vminvq_u32, aarch64_neon_uminv, AddRetType | Add1ArgType),
 4948   NEONMAP1(vmull_p64, aarch64_neon_pmull64, 0),
 4949   NEONMAP1(vmulxd_f64, aarch64_neon_fmulx, Add1ArgType),
 4950   NEONMAP1(vmulxs_f32, aarch64_neon_fmulx, Add1ArgType),
 4951   NEONMAP1(vpaddd_s64, aarch64_neon_uaddv, AddRetType | Add1ArgType),
 4952   NEONMAP1(vpaddd_u64, aarch64_neon_uaddv, AddRetType | Add1ArgType),
 4953   NEONMAP1(vpmaxnmqd_f64, aarch64_neon_fmaxnmv, AddRetType | Add1ArgType),
 4954   NEONMAP1(vpmaxnms_f32, aarch64_neon_fmaxnmv, AddRetType | Add1ArgType),
 4955   NEONMAP1(vpmaxqd_f64, aarch64_neon_fmaxv, AddRetType | Add1ArgType),
 4956   NEONMAP1(vpmaxs_f32, aarch64_neon_fmaxv, AddRetType | Add1ArgType),
 4957   NEONMAP1(vpminnmqd_f64, aarch64_neon_fminnmv, AddRetType | Add1ArgType),
 4958   NEONMAP1(vpminnms_f32, aarch64_neon_fminnmv, AddRetType | Add1ArgType),
 4959   NEONMAP1(vpminqd_f64, aarch64_neon_fminv, AddRetType | Add1ArgType),
 4960   NEONMAP1(vpmins_f32, aarch64_neon_fminv, AddRetType | Add1ArgType),
 4961   NEONMAP1(vqabsb_s8, aarch64_neon_sqabs, Vectorize1ArgType | Use64BitVectors),
 4962   NEONMAP1(vqabsd_s64, aarch64_neon_sqabs, Add1ArgType),
 4963   NEONMAP1(vqabsh_s16, aarch64_neon_sqabs, Vectorize1ArgType | Use64BitVectors),
 4964   NEONMAP1(vqabss_s32, aarch64_neon_sqabs, Add1ArgType),
 4965   NEONMAP1(vqaddb_s8, aarch64_neon_sqadd, Vectorize1ArgType | Use64BitVectors),
 4966   NEONMAP1(vqaddb_u8, aarch64_neon_uqadd, Vectorize1ArgType | Use64BitVectors),
 4967   NEONMAP1(vqaddd_s64, aarch64_neon_sqadd, Add1ArgType),
 4968   NEONMAP1(vqaddd_u64, aarch64_neon_uqadd, Add1ArgType),
 4969   NEONMAP1(vqaddh_s16, aarch64_neon_sqadd, Vectorize1ArgType | Use64BitVectors),
 4970   NEONMAP1(vqaddh_u16, aarch64_neon_uqadd, Vectorize1ArgType | Use64BitVectors),
 4971   NEONMAP1(vqadds_s32, aarch64_neon_sqadd, Add1ArgType),
 4972   NEONMAP1(vqadds_u32, aarch64_neon_uqadd, Add1ArgType),
 4973   NEONMAP1(vqdmulhh_s16, aarch64_neon_sqdmulh, Vectorize1ArgType | Use64BitVectors),
 4974   NEONMAP1(vqdmulhs_s32, aarch64_neon_sqdmulh, Add1ArgType),
 4975   NEONMAP1(vqdmullh_s16, aarch64_neon_sqdmull, VectorRet | Use128BitVectors),
 4976   NEONMAP1(vqdmulls_s32, aarch64_neon_sqdmulls_scalar, 0),
 4977   NEONMAP1(vqmovnd_s64, aarch64_neon_scalar_sqxtn, AddRetType | Add1ArgType),
 4978   NEONMAP1(vqmovnd_u64, aarch64_neon_scalar_uqxtn, AddRetType | Add1ArgType),
 4979   NEONMAP1(vqmovnh_s16, aarch64_neon_sqxtn, VectorRet | Use64BitVectors),
 4980   NEONMAP1(vqmovnh_u16, aarch64_neon_uqxtn, VectorRet | Use64BitVectors),
 4981   NEONMAP1(vqmovns_s32, aarch64_neon_sqxtn, VectorRet | Use64BitVectors),
 4982   NEONMAP1(vqmovns_u32, aarch64_neon_uqxtn, VectorRet | Use64BitVectors),
 4983   NEONMAP1(vqmovund_s64, aarch64_neon_scalar_sqxtun, AddRetType | Add1ArgType),
 4984   NEONMAP1(vqmovunh_s16, aarch64_neon_sqxtun, VectorRet | Use64BitVectors),
 4985   NEONMAP1(vqmovuns_s32, aarch64_neon_sqxtun, VectorRet | Use64BitVectors),
 4986   NEONMAP1(vqnegb_s8, aarch64_neon_sqneg, Vectorize1ArgType | Use64BitVectors),
 4987   NEONMAP1(vqnegd_s64, aarch64_neon_sqneg, Add1ArgType),
 4988   NEONMAP1(vqnegh_s16, aarch64_neon_sqneg, Vectorize1ArgType | Use64BitVectors),
 4989   NEONMAP1(vqnegs_s32, aarch64_neon_sqneg, Add1ArgType),
 4990   NEONMAP1(vqrdmulhh_s16, aarch64_neon_sqrdmulh, Vectorize1ArgType | Use64BitVectors),
 4991   NEONMAP1(vqrdmulhs_s32, aarch64_neon_sqrdmulh, Add1ArgType),
 4992   NEONMAP1(vqrshlb_s8, aarch64_neon_sqrshl, Vectorize1ArgType | Use64BitVectors),
 4993   NEONMAP1(vqrshlb_u8, aarch64_neon_uqrshl, Vectorize1ArgType | Use64BitVectors),
 4994   NEONMAP1(vqrshld_s64, aarch64_neon_sqrshl, Add1ArgType),
 4995   NEONMAP1(vqrshld_u64, aarch64_neon_uqrshl, Add1ArgType),
 4996   NEONMAP1(vqrshlh_s16, aarch64_neon_sqrshl, Vectorize1ArgType | Use64BitVectors),
 4997   NEONMAP1(vqrshlh_u16, aarch64_neon_uqrshl, Vectorize1ArgType | Use64BitVectors),
 4998   NEONMAP1(vqrshls_s32, aarch64_neon_sqrshl, Add1ArgType),
 4999   NEONMAP1(vqrshls_u32, aarch64_neon_uqrshl, Add1ArgType),
 5000   NEONMAP1(vqrshrnd_n_s64, aarch64_neon_sqrshrn, AddRetType),
 5001   NEONMAP1(vqrshrnd_n_u64, aarch64_neon_uqrshrn, AddRetType),
 5002   NEONMAP1(vqrshrnh_n_s16, aarch64_neon_sqrshrn, VectorRet | Use64BitVectors),
 5003   NEONMAP1(vqrshrnh_n_u16, aarch64_neon_uqrshrn, VectorRet | Use64BitVectors),
 5004   NEONMAP1(vqrshrns_n_s32, aarch64_neon_sqrshrn, VectorRet | Use64BitVectors),
 5005   NEONMAP1(vqrshrns_n_u32, aarch64_neon_uqrshrn, VectorRet | Use64BitVectors),
 5006   NEONMAP1(vqrshrund_n_s64, aarch64_neon_sqrshrun, AddRetType),
 5007   NEONMAP1(vqrshrunh_n_s16, aarch64_neon_sqrshrun, VectorRet | Use64BitVectors),
 5008   NEONMAP1(vqrshruns_n_s32, aarch64_neon_sqrshrun, VectorRet | Use64BitVectors),
 5009   NEONMAP1(vqshlb_n_s8, aarch64_neon_sqshl, Vectorize1ArgType | Use64BitVectors),
 5010   NEONMAP1(vqshlb_n_u8, aarch64_neon_uqshl, Vectorize1ArgType | Use64BitVectors),
 5011   NEONMAP1(vqshlb_s8, aarch64_neon_sqshl, Vectorize1ArgType | Use64BitVectors),
 5012   NEONMAP1(vqshlb_u8, aarch64_neon_uqshl, Vectorize1ArgType | Use64BitVectors),
 5013   NEONMAP1(vqshld_s64, aarch64_neon_sqshl, Add1ArgType),
 5014   NEONMAP1(vqshld_u64, aarch64_neon_uqshl, Add1ArgType),
 5015   NEONMAP1(vqshlh_n_s16, aarch64_neon_sqshl, Vectorize1ArgType | Use64BitVectors),
 5016   NEONMAP1(vqshlh_n_u16, aarch64_neon_uqshl, Vectorize1ArgType | Use64BitVectors),
 5017   NEONMAP1(vqshlh_s16, aarch64_neon_sqshl, Vectorize1ArgType | Use64BitVectors),
 5018   NEONMAP1(vqshlh_u16, aarch64_neon_uqshl, Vectorize1ArgType | Use64BitVectors),
 5019   NEONMAP1(vqshls_n_s32, aarch64_neon_sqshl, Add1ArgType),
 5020   NEONMAP1(vqshls_n_u32, aarch64_neon_uqshl, Add1ArgType),
 5021   NEONMAP1(vqshls_s32, aarch64_neon_sqshl, Add1ArgType),
 5022   NEONMAP1(vqshls_u32, aarch64_neon_uqshl, Add1ArgType),
 5023   NEONMAP1(vqshlub_n_s8, aarch64_neon_sqshlu, Vectorize1ArgType | Use64BitVectors),
 5024   NEONMAP1(vqshluh_n_s16, aarch64_neon_sqshlu, Vectorize1ArgType | Use64BitVectors),
 5025   NEONMAP1(vqshlus_n_s32, aarch64_neon_sqshlu, Add1ArgType),
 5026   NEONMAP1(vqshrnd_n_s64, aarch64_neon_sqshrn, AddRetType),
 5027   NEONMAP1(vqshrnd_n_u64, aarch64_neon_uqshrn, AddRetType),
 5028   NEONMAP1(vqshrnh_n_s16, aarch64_neon_sqshrn, VectorRet | Use64BitVectors),
 5029   NEONMAP1(vqshrnh_n_u16, aarch64_neon_uqshrn, VectorRet | Use64BitVectors),
 5030   NEONMAP1(vqshrns_n_s32, aarch64_neon_sqshrn, VectorRet | Use64BitVectors),
 5031   NEONMAP1(vqshrns_n_u32, aarch64_neon_uqshrn, VectorRet | Use64BitVectors),
 5032   NEONMAP1(vqshrund_n_s64, aarch64_neon_sqshrun, AddRetType),
 5033   NEONMAP1(vqshrunh_n_s16, aarch64_neon_sqshrun, VectorRet | Use64BitVectors),
 5034   NEONMAP1(vqshruns_n_s32, aarch64_neon_sqshrun, VectorRet | Use64BitVectors),
 5035   NEONMAP1(vqsubb_s8, aarch64_neon_sqsub, Vectorize1ArgType | Use64BitVectors),
 5036   NEONMAP1(vqsubb_u8, aarch64_neon_uqsub, Vectorize1ArgType | Use64BitVectors),
 5037   NEONMAP1(vqsubd_s64, aarch64_neon_sqsub, Add1ArgType),
 5038   NEONMAP1(vqsubd_u64, aarch64_neon_uqsub, Add1ArgType),
 5039   NEONMAP1(vqsubh_s16, aarch64_neon_sqsub, Vectorize1ArgType | Use64BitVectors),
 5040   NEONMAP1(vqsubh_u16, aarch64_neon_uqsub, Vectorize1ArgType | Use64BitVectors),
 5041   NEONMAP1(vqsubs_s32, aarch64_neon_sqsub, Add1ArgType),
 5042   NEONMAP1(vqsubs_u32, aarch64_neon_uqsub, Add1ArgType),
 5043   NEONMAP1(vrecped_f64, aarch64_neon_frecpe, Add1ArgType),
 5044   NEONMAP1(vrecpes_f32, aarch64_neon_frecpe, Add1ArgType),
 5045   NEONMAP1(vrecpxd_f64, aarch64_neon_frecpx, Add1ArgType),
 5046   NEONMAP1(vrecpxs_f32, aarch64_neon_frecpx, Add1ArgType),
 5047   NEONMAP1(vrshld_s64, aarch64_neon_srshl, Add1ArgType),
 5048   NEONMAP1(vrshld_u64, aarch64_neon_urshl, Add1ArgType),
 5049   NEONMAP1(vrsqrted_f64, aarch64_neon_frsqrte, Add1ArgType),
 5050   NEONMAP1(vrsqrtes_f32, aarch64_neon_frsqrte, Add1ArgType),
 5051   NEONMAP1(vrsqrtsd_f64, aarch64_neon_frsqrts, Add1ArgType),
 5052   NEONMAP1(vrsqrtss_f32, aarch64_neon_frsqrts, Add1ArgType),
 5053   NEONMAP1(vsha1cq_u32, aarch64_crypto_sha1c, 0),
 5054   NEONMAP1(vsha1h_u32, aarch64_crypto_sha1h, 0),
 5055   NEONMAP1(vsha1mq_u32, aarch64_crypto_sha1m, 0),
 5056   NEONMAP1(vsha1pq_u32, aarch64_crypto_sha1p, 0),
 5057   NEONMAP1(vshld_s64, aarch64_neon_sshl, Add1ArgType),
 5058   NEONMAP1(vshld_u64, aarch64_neon_ushl, Add1ArgType),
 5059   NEONMAP1(vslid_n_s64, aarch64_neon_vsli, Vectorize1ArgType),
 5060   NEONMAP1(vslid_n_u64, aarch64_neon_vsli, Vectorize1ArgType),
 5061   NEONMAP1(vsqaddb_u8, aarch64_neon_usqadd, Vectorize1ArgType | Use64BitVectors),
 5062   NEONMAP1(vsqaddd_u64, aarch64_neon_usqadd, Add1ArgType),
 5063   NEONMAP1(vsqaddh_u16, aarch64_neon_usqadd, Vectorize1ArgType | Use64BitVectors),
 5064   NEONMAP1(vsqadds_u32, aarch64_neon_usqadd, Add1ArgType),
 5065   NEONMAP1(vsrid_n_s64, aarch64_neon_vsri, Vectorize1ArgType),
 5066   NEONMAP1(vsrid_n_u64, aarch64_neon_vsri, Vectorize1ArgType),
 5067   NEONMAP1(vuqaddb_s8, aarch64_neon_suqadd, Vectorize1ArgType | Use64BitVectors),
 5068   NEONMAP1(vuqaddd_s64, aarch64_neon_suqadd, Add1ArgType),
 5069   NEONMAP1(vuqaddh_s16, aarch64_neon_suqadd, Vectorize1ArgType | Use64BitVectors),
 5070   NEONMAP1(vuqadds_s32, aarch64_neon_suqadd, Add1ArgType),
 5072   NEONMAP1(vabdh_f16, aarch64_sisd_fabd, Add1ArgType),
 5073   NEONMAP1(vcvtah_s32_f16, aarch64_neon_fcvtas, AddRetType | Add1ArgType),
 5074   NEONMAP1(vcvtah_s64_f16, aarch64_neon_fcvtas, AddRetType | Add1ArgType),
 5075   NEONMAP1(vcvtah_u32_f16, aarch64_neon_fcvtau, AddRetType | Add1ArgType),
 5076   NEONMAP1(vcvtah_u64_f16, aarch64_neon_fcvtau, AddRetType | Add1ArgType),
 5077   NEONMAP1(vcvth_n_f16_s32, aarch64_neon_vcvtfxs2fp, AddRetType | Add1ArgType),
 5078   NEONMAP1(vcvth_n_f16_s64, aarch64_neon_vcvtfxs2fp, AddRetType | Add1ArgType),
 5079   NEONMAP1(vcvth_n_f16_u32, aarch64_neon_vcvtfxu2fp, AddRetType | Add1ArgType),
 5080   NEONMAP1(vcvth_n_f16_u64, aarch64_neon_vcvtfxu2fp, AddRetType | Add1ArgType),
 5081   NEONMAP1(vcvth_n_s32_f16, aarch64_neon_vcvtfp2fxs, AddRetType | Add1ArgType),
 5082   NEONMAP1(vcvth_n_s64_f16, aarch64_neon_vcvtfp2fxs, AddRetType | Add1ArgType),
 5083   NEONMAP1(vcvth_n_u32_f16, aarch64_neon_vcvtfp2fxu, AddRetType | Add1ArgType),
 5084   NEONMAP1(vcvth_n_u64_f16, aarch64_neon_vcvtfp2fxu, AddRetType | Add1ArgType),
 5085   NEONMAP1(vcvtmh_s32_f16, aarch64_neon_fcvtms, AddRetType | Add1ArgType),
 5086   NEONMAP1(vcvtmh_s64_f16, aarch64_neon_fcvtms, AddRetType | Add1ArgType),
 5087   NEONMAP1(vcvtmh_u32_f16, aarch64_neon_fcvtmu, AddRetType | Add1ArgType),
 5088   NEONMAP1(vcvtmh_u64_f16, aarch64_neon_fcvtmu, AddRetType | Add1ArgType),
 5089   NEONMAP1(vcvtnh_s32_f16, aarch64_neon_fcvtns, AddRetType | Add1ArgType),
 5090   NEONMAP1(vcvtnh_s64_f16, aarch64_neon_fcvtns, AddRetType | Add1ArgType),
 5091   NEONMAP1(vcvtnh_u32_f16, aarch64_neon_fcvtnu, AddRetType | Add1ArgType),
 5092   NEONMAP1(vcvtnh_u64_f16, aarch64_neon_fcvtnu, AddRetType | Add1ArgType),
 5093   NEONMAP1(vcvtph_s32_f16, aarch64_neon_fcvtps, AddRetType | Add1ArgType),
 5094   NEONMAP1(vcvtph_s64_f16, aarch64_neon_fcvtps, AddRetType | Add1ArgType),
 5095   NEONMAP1(vcvtph_u32_f16, aarch64_neon_fcvtpu, AddRetType | Add1ArgType),
 5096   NEONMAP1(vcvtph_u64_f16, aarch64_neon_fcvtpu, AddRetType | Add1ArgType),
 5097   NEONMAP1(vmulxh_f16, aarch64_neon_fmulx, Add1ArgType),
 5098   NEONMAP1(vrecpeh_f16, aarch64_neon_frecpe, Add1ArgType),
 5099   NEONMAP1(vrecpxh_f16, aarch64_neon_frecpx, Add1ArgType),
 5100   NEONMAP1(vrsqrteh_f16, aarch64_neon_frsqrte, Add1ArgType),
 5101   NEONMAP1(vrsqrtsh_f16, aarch64_neon_frsqrts, Add1ArgType),