Mercurial > hg > CbC > CbC_gcc
comparison gcc/config/arm/arm_neon.h @ 55:77e2b8dfacca gcc-4.4.5
update it from 4.4.3 to 4.5.0
| author | ryoma <e075725@ie.u-ryukyu.ac.jp> |
|---|---|
| date | Fri, 12 Feb 2010 23:39:51 +0900 |
| parents | a06113de4d67 |
| children | f6334be47118 |
comparison
equal
deleted
inserted
replaced
| 52:c156f1bd5cd9 | 55:77e2b8dfacca |
|---|---|
| 59 typedef __builtin_neon_uqi uint8x16_t __attribute__ ((__vector_size__ (16))); | 59 typedef __builtin_neon_uqi uint8x16_t __attribute__ ((__vector_size__ (16))); |
| 60 typedef __builtin_neon_uhi uint16x8_t __attribute__ ((__vector_size__ (16))); | 60 typedef __builtin_neon_uhi uint16x8_t __attribute__ ((__vector_size__ (16))); |
| 61 typedef __builtin_neon_usi uint32x4_t __attribute__ ((__vector_size__ (16))); | 61 typedef __builtin_neon_usi uint32x4_t __attribute__ ((__vector_size__ (16))); |
| 62 typedef __builtin_neon_udi uint64x2_t __attribute__ ((__vector_size__ (16))); | 62 typedef __builtin_neon_udi uint64x2_t __attribute__ ((__vector_size__ (16))); |
| 63 | 63 |
| 64 typedef __builtin_neon_sf float32_t; | 64 typedef float float32_t; |
| 65 typedef __builtin_neon_poly8 poly8_t; | 65 typedef __builtin_neon_poly8 poly8_t; |
| 66 typedef __builtin_neon_poly16 poly16_t; | 66 typedef __builtin_neon_poly16 poly16_t; |
| 67 | 67 |
| 68 typedef struct int8x8x2_t | 68 typedef struct int8x8x2_t |
| 69 { | 69 { |
| 5083 } | 5083 } |
| 5084 | 5084 |
| 5085 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 5085 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 5086 vset_lane_f32 (float32_t __a, float32x2_t __b, const int __c) | 5086 vset_lane_f32 (float32_t __a, float32x2_t __b, const int __c) |
| 5087 { | 5087 { |
| 5088 return (float32x2_t)__builtin_neon_vset_lanev2sf (__a, __b, __c); | 5088 return (float32x2_t)__builtin_neon_vset_lanev2sf ((__builtin_neon_sf) __a, __b, __c); |
| 5089 } | 5089 } |
| 5090 | 5090 |
| 5091 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) | 5091 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) |
| 5092 vset_lane_u8 (uint8_t __a, uint8x8_t __b, const int __c) | 5092 vset_lane_u8 (uint8_t __a, uint8x8_t __b, const int __c) |
| 5093 { | 5093 { |
| 5149 } | 5149 } |
| 5150 | 5150 |
| 5151 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 5151 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 5152 vsetq_lane_f32 (float32_t __a, float32x4_t __b, const int __c) | 5152 vsetq_lane_f32 (float32_t __a, float32x4_t __b, const int __c) |
| 5153 { | 5153 { |
| 5154 return (float32x4_t)__builtin_neon_vset_lanev4sf (__a, __b, __c); | 5154 return (float32x4_t)__builtin_neon_vset_lanev4sf ((__builtin_neon_sf) __a, __b, __c); |
| 5155 } | 5155 } |
| 5156 | 5156 |
| 5157 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) | 5157 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) |
| 5158 vsetq_lane_u8 (uint8_t __a, uint8x16_t __b, const int __c) | 5158 vsetq_lane_u8 (uint8_t __a, uint8x16_t __b, const int __c) |
| 5159 { | 5159 { |
| 5281 } | 5281 } |
| 5282 | 5282 |
| 5283 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 5283 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 5284 vdup_n_f32 (float32_t __a) | 5284 vdup_n_f32 (float32_t __a) |
| 5285 { | 5285 { |
| 5286 return (float32x2_t)__builtin_neon_vdup_nv2sf (__a); | 5286 return (float32x2_t)__builtin_neon_vdup_nv2sf ((__builtin_neon_sf) __a); |
| 5287 } | 5287 } |
| 5288 | 5288 |
| 5289 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) | 5289 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) |
| 5290 vdup_n_u8 (uint8_t __a) | 5290 vdup_n_u8 (uint8_t __a) |
| 5291 { | 5291 { |
| 5347 } | 5347 } |
| 5348 | 5348 |
| 5349 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 5349 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 5350 vdupq_n_f32 (float32_t __a) | 5350 vdupq_n_f32 (float32_t __a) |
| 5351 { | 5351 { |
| 5352 return (float32x4_t)__builtin_neon_vdup_nv4sf (__a); | 5352 return (float32x4_t)__builtin_neon_vdup_nv4sf ((__builtin_neon_sf) __a); |
| 5353 } | 5353 } |
| 5354 | 5354 |
| 5355 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) | 5355 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) |
| 5356 vdupq_n_u8 (uint8_t __a) | 5356 vdupq_n_u8 (uint8_t __a) |
| 5357 { | 5357 { |
| 5413 } | 5413 } |
| 5414 | 5414 |
| 5415 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 5415 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 5416 vmov_n_f32 (float32_t __a) | 5416 vmov_n_f32 (float32_t __a) |
| 5417 { | 5417 { |
| 5418 return (float32x2_t)__builtin_neon_vdup_nv2sf (__a); | 5418 return (float32x2_t)__builtin_neon_vdup_nv2sf ((__builtin_neon_sf) __a); |
| 5419 } | 5419 } |
| 5420 | 5420 |
| 5421 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) | 5421 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) |
| 5422 vmov_n_u8 (uint8_t __a) | 5422 vmov_n_u8 (uint8_t __a) |
| 5423 { | 5423 { |
| 5479 } | 5479 } |
| 5480 | 5480 |
| 5481 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 5481 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 5482 vmovq_n_f32 (float32_t __a) | 5482 vmovq_n_f32 (float32_t __a) |
| 5483 { | 5483 { |
| 5484 return (float32x4_t)__builtin_neon_vdup_nv4sf (__a); | 5484 return (float32x4_t)__builtin_neon_vdup_nv4sf ((__builtin_neon_sf) __a); |
| 5485 } | 5485 } |
| 5486 | 5486 |
| 5487 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) | 5487 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) |
| 5488 vmovq_n_u8 (uint8_t __a) | 5488 vmovq_n_u8 (uint8_t __a) |
| 5489 { | 5489 { |
| 6589 } | 6589 } |
| 6590 | 6590 |
| 6591 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 6591 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 6592 vmul_n_f32 (float32x2_t __a, float32_t __b) | 6592 vmul_n_f32 (float32x2_t __a, float32_t __b) |
| 6593 { | 6593 { |
| 6594 return (float32x2_t)__builtin_neon_vmul_nv2sf (__a, __b, 3); | 6594 return (float32x2_t)__builtin_neon_vmul_nv2sf (__a, (__builtin_neon_sf) __b, 3); |
| 6595 } | 6595 } |
| 6596 | 6596 |
| 6597 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__)) | 6597 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__)) |
| 6598 vmul_n_u16 (uint16x4_t __a, uint16_t __b) | 6598 vmul_n_u16 (uint16x4_t __a, uint16_t __b) |
| 6599 { | 6599 { |
| 6619 } | 6619 } |
| 6620 | 6620 |
| 6621 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 6621 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 6622 vmulq_n_f32 (float32x4_t __a, float32_t __b) | 6622 vmulq_n_f32 (float32x4_t __a, float32_t __b) |
| 6623 { | 6623 { |
| 6624 return (float32x4_t)__builtin_neon_vmul_nv4sf (__a, __b, 3); | 6624 return (float32x4_t)__builtin_neon_vmul_nv4sf (__a, (__builtin_neon_sf) __b, 3); |
| 6625 } | 6625 } |
| 6626 | 6626 |
| 6627 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__)) | 6627 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__)) |
| 6628 vmulq_n_u16 (uint16x8_t __a, uint16_t __b) | 6628 vmulq_n_u16 (uint16x8_t __a, uint16_t __b) |
| 6629 { | 6629 { |
| 6733 } | 6733 } |
| 6734 | 6734 |
| 6735 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 6735 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 6736 vmla_n_f32 (float32x2_t __a, float32x2_t __b, float32_t __c) | 6736 vmla_n_f32 (float32x2_t __a, float32x2_t __b, float32_t __c) |
| 6737 { | 6737 { |
| 6738 return (float32x2_t)__builtin_neon_vmla_nv2sf (__a, __b, __c, 3); | 6738 return (float32x2_t)__builtin_neon_vmla_nv2sf (__a, __b, (__builtin_neon_sf) __c, 3); |
| 6739 } | 6739 } |
| 6740 | 6740 |
| 6741 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__)) | 6741 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__)) |
| 6742 vmla_n_u16 (uint16x4_t __a, uint16x4_t __b, uint16_t __c) | 6742 vmla_n_u16 (uint16x4_t __a, uint16x4_t __b, uint16_t __c) |
| 6743 { | 6743 { |
| 6763 } | 6763 } |
| 6764 | 6764 |
| 6765 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 6765 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 6766 vmlaq_n_f32 (float32x4_t __a, float32x4_t __b, float32_t __c) | 6766 vmlaq_n_f32 (float32x4_t __a, float32x4_t __b, float32_t __c) |
| 6767 { | 6767 { |
| 6768 return (float32x4_t)__builtin_neon_vmla_nv4sf (__a, __b, __c, 3); | 6768 return (float32x4_t)__builtin_neon_vmla_nv4sf (__a, __b, (__builtin_neon_sf) __c, 3); |
| 6769 } | 6769 } |
| 6770 | 6770 |
| 6771 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__)) | 6771 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__)) |
| 6772 vmlaq_n_u16 (uint16x8_t __a, uint16x8_t __b, uint16_t __c) | 6772 vmlaq_n_u16 (uint16x8_t __a, uint16x8_t __b, uint16_t __c) |
| 6773 { | 6773 { |
| 6829 } | 6829 } |
| 6830 | 6830 |
| 6831 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 6831 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 6832 vmls_n_f32 (float32x2_t __a, float32x2_t __b, float32_t __c) | 6832 vmls_n_f32 (float32x2_t __a, float32x2_t __b, float32_t __c) |
| 6833 { | 6833 { |
| 6834 return (float32x2_t)__builtin_neon_vmls_nv2sf (__a, __b, __c, 3); | 6834 return (float32x2_t)__builtin_neon_vmls_nv2sf (__a, __b, (__builtin_neon_sf) __c, 3); |
| 6835 } | 6835 } |
| 6836 | 6836 |
| 6837 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__)) | 6837 __extension__ static __inline uint16x4_t __attribute__ ((__always_inline__)) |
| 6838 vmls_n_u16 (uint16x4_t __a, uint16x4_t __b, uint16_t __c) | 6838 vmls_n_u16 (uint16x4_t __a, uint16x4_t __b, uint16_t __c) |
| 6839 { | 6839 { |
| 6859 } | 6859 } |
| 6860 | 6860 |
| 6861 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 6861 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 6862 vmlsq_n_f32 (float32x4_t __a, float32x4_t __b, float32_t __c) | 6862 vmlsq_n_f32 (float32x4_t __a, float32x4_t __b, float32_t __c) |
| 6863 { | 6863 { |
| 6864 return (float32x4_t)__builtin_neon_vmls_nv4sf (__a, __b, __c, 3); | 6864 return (float32x4_t)__builtin_neon_vmls_nv4sf (__a, __b, (__builtin_neon_sf) __c, 3); |
| 6865 } | 6865 } |
| 6866 | 6866 |
| 6867 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__)) | 6867 __extension__ static __inline uint16x8_t __attribute__ ((__always_inline__)) |
| 6868 vmlsq_n_u16 (uint16x8_t __a, uint16x8_t __b, uint16_t __c) | 6868 vmlsq_n_u16 (uint16x8_t __a, uint16x8_t __b, uint16_t __c) |
| 6869 { | 6869 { |
| 7849 } | 7849 } |
| 7850 | 7850 |
| 7851 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 7851 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 7852 vld1_f32 (const float32_t * __a) | 7852 vld1_f32 (const float32_t * __a) |
| 7853 { | 7853 { |
| 7854 return (float32x2_t)__builtin_neon_vld1v2sf (__a); | 7854 return (float32x2_t)__builtin_neon_vld1v2sf ((const __builtin_neon_sf *) __a); |
| 7855 } | 7855 } |
| 7856 | 7856 |
| 7857 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) | 7857 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) |
| 7858 vld1_u8 (const uint8_t * __a) | 7858 vld1_u8 (const uint8_t * __a) |
| 7859 { | 7859 { |
| 7915 } | 7915 } |
| 7916 | 7916 |
| 7917 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 7917 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 7918 vld1q_f32 (const float32_t * __a) | 7918 vld1q_f32 (const float32_t * __a) |
| 7919 { | 7919 { |
| 7920 return (float32x4_t)__builtin_neon_vld1v4sf (__a); | 7920 return (float32x4_t)__builtin_neon_vld1v4sf ((const __builtin_neon_sf *) __a); |
| 7921 } | 7921 } |
| 7922 | 7922 |
| 7923 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) | 7923 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) |
| 7924 vld1q_u8 (const uint8_t * __a) | 7924 vld1q_u8 (const uint8_t * __a) |
| 7925 { | 7925 { |
| 7975 } | 7975 } |
| 7976 | 7976 |
| 7977 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 7977 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 7978 vld1_lane_f32 (const float32_t * __a, float32x2_t __b, const int __c) | 7978 vld1_lane_f32 (const float32_t * __a, float32x2_t __b, const int __c) |
| 7979 { | 7979 { |
| 7980 return (float32x2_t)__builtin_neon_vld1_lanev2sf (__a, __b, __c); | 7980 return (float32x2_t)__builtin_neon_vld1_lanev2sf ((const __builtin_neon_sf *) __a, __b, __c); |
| 7981 } | 7981 } |
| 7982 | 7982 |
| 7983 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) | 7983 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) |
| 7984 vld1_lane_u8 (const uint8_t * __a, uint8x8_t __b, const int __c) | 7984 vld1_lane_u8 (const uint8_t * __a, uint8x8_t __b, const int __c) |
| 7985 { | 7985 { |
| 8041 } | 8041 } |
| 8042 | 8042 |
| 8043 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 8043 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 8044 vld1q_lane_f32 (const float32_t * __a, float32x4_t __b, const int __c) | 8044 vld1q_lane_f32 (const float32_t * __a, float32x4_t __b, const int __c) |
| 8045 { | 8045 { |
| 8046 return (float32x4_t)__builtin_neon_vld1_lanev4sf (__a, __b, __c); | 8046 return (float32x4_t)__builtin_neon_vld1_lanev4sf ((const __builtin_neon_sf *) __a, __b, __c); |
| 8047 } | 8047 } |
| 8048 | 8048 |
| 8049 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) | 8049 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) |
| 8050 vld1q_lane_u8 (const uint8_t * __a, uint8x16_t __b, const int __c) | 8050 vld1q_lane_u8 (const uint8_t * __a, uint8x16_t __b, const int __c) |
| 8051 { | 8051 { |
| 8107 } | 8107 } |
| 8108 | 8108 |
| 8109 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) | 8109 __extension__ static __inline float32x2_t __attribute__ ((__always_inline__)) |
| 8110 vld1_dup_f32 (const float32_t * __a) | 8110 vld1_dup_f32 (const float32_t * __a) |
| 8111 { | 8111 { |
| 8112 return (float32x2_t)__builtin_neon_vld1_dupv2sf (__a); | 8112 return (float32x2_t)__builtin_neon_vld1_dupv2sf ((const __builtin_neon_sf *) __a); |
| 8113 } | 8113 } |
| 8114 | 8114 |
| 8115 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) | 8115 __extension__ static __inline uint8x8_t __attribute__ ((__always_inline__)) |
| 8116 vld1_dup_u8 (const uint8_t * __a) | 8116 vld1_dup_u8 (const uint8_t * __a) |
| 8117 { | 8117 { |
| 8173 } | 8173 } |
| 8174 | 8174 |
| 8175 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) | 8175 __extension__ static __inline float32x4_t __attribute__ ((__always_inline__)) |
| 8176 vld1q_dup_f32 (const float32_t * __a) | 8176 vld1q_dup_f32 (const float32_t * __a) |
| 8177 { | 8177 { |
| 8178 return (float32x4_t)__builtin_neon_vld1_dupv4sf (__a); | 8178 return (float32x4_t)__builtin_neon_vld1_dupv4sf ((const __builtin_neon_sf *) __a); |
| 8179 } | 8179 } |
| 8180 | 8180 |
| 8181 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) | 8181 __extension__ static __inline uint8x16_t __attribute__ ((__always_inline__)) |
| 8182 vld1q_dup_u8 (const uint8_t * __a) | 8182 vld1q_dup_u8 (const uint8_t * __a) |
| 8183 { | 8183 { |
| 8245 } | 8245 } |
| 8246 | 8246 |
| 8247 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8247 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8248 vst1_f32 (float32_t * __a, float32x2_t __b) | 8248 vst1_f32 (float32_t * __a, float32x2_t __b) |
| 8249 { | 8249 { |
| 8250 __builtin_neon_vst1v2sf (__a, __b); | 8250 __builtin_neon_vst1v2sf ((__builtin_neon_sf *) __a, __b); |
| 8251 } | 8251 } |
| 8252 | 8252 |
| 8253 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8253 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8254 vst1_u8 (uint8_t * __a, uint8x8_t __b) | 8254 vst1_u8 (uint8_t * __a, uint8x8_t __b) |
| 8255 { | 8255 { |
| 8311 } | 8311 } |
| 8312 | 8312 |
| 8313 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8313 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8314 vst1q_f32 (float32_t * __a, float32x4_t __b) | 8314 vst1q_f32 (float32_t * __a, float32x4_t __b) |
| 8315 { | 8315 { |
| 8316 __builtin_neon_vst1v4sf (__a, __b); | 8316 __builtin_neon_vst1v4sf ((__builtin_neon_sf *) __a, __b); |
| 8317 } | 8317 } |
| 8318 | 8318 |
| 8319 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8319 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8320 vst1q_u8 (uint8_t * __a, uint8x16_t __b) | 8320 vst1q_u8 (uint8_t * __a, uint8x16_t __b) |
| 8321 { | 8321 { |
| 8371 } | 8371 } |
| 8372 | 8372 |
| 8373 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8373 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8374 vst1_lane_f32 (float32_t * __a, float32x2_t __b, const int __c) | 8374 vst1_lane_f32 (float32_t * __a, float32x2_t __b, const int __c) |
| 8375 { | 8375 { |
| 8376 __builtin_neon_vst1_lanev2sf (__a, __b, __c); | 8376 __builtin_neon_vst1_lanev2sf ((__builtin_neon_sf *) __a, __b, __c); |
| 8377 } | 8377 } |
| 8378 | 8378 |
| 8379 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8379 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8380 vst1_lane_u8 (uint8_t * __a, uint8x8_t __b, const int __c) | 8380 vst1_lane_u8 (uint8_t * __a, uint8x8_t __b, const int __c) |
| 8381 { | 8381 { |
| 8437 } | 8437 } |
| 8438 | 8438 |
| 8439 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8439 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8440 vst1q_lane_f32 (float32_t * __a, float32x4_t __b, const int __c) | 8440 vst1q_lane_f32 (float32_t * __a, float32x4_t __b, const int __c) |
| 8441 { | 8441 { |
| 8442 __builtin_neon_vst1_lanev4sf (__a, __b, __c); | 8442 __builtin_neon_vst1_lanev4sf ((__builtin_neon_sf *) __a, __b, __c); |
| 8443 } | 8443 } |
| 8444 | 8444 |
| 8445 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8445 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8446 vst1q_lane_u8 (uint8_t * __a, uint8x16_t __b, const int __c) | 8446 vst1q_lane_u8 (uint8_t * __a, uint8x16_t __b, const int __c) |
| 8447 { | 8447 { |
| 8510 | 8510 |
| 8511 __extension__ static __inline float32x2x2_t __attribute__ ((__always_inline__)) | 8511 __extension__ static __inline float32x2x2_t __attribute__ ((__always_inline__)) |
| 8512 vld2_f32 (const float32_t * __a) | 8512 vld2_f32 (const float32_t * __a) |
| 8513 { | 8513 { |
| 8514 union { float32x2x2_t __i; __builtin_neon_ti __o; } __rv; | 8514 union { float32x2x2_t __i; __builtin_neon_ti __o; } __rv; |
| 8515 __rv.__o = __builtin_neon_vld2v2sf (__a); | 8515 __rv.__o = __builtin_neon_vld2v2sf ((const __builtin_neon_sf *) __a); |
| 8516 return __rv.__i; | 8516 return __rv.__i; |
| 8517 } | 8517 } |
| 8518 | 8518 |
| 8519 __extension__ static __inline uint8x8x2_t __attribute__ ((__always_inline__)) | 8519 __extension__ static __inline uint8x8x2_t __attribute__ ((__always_inline__)) |
| 8520 vld2_u8 (const uint8_t * __a) | 8520 vld2_u8 (const uint8_t * __a) |
| 8598 | 8598 |
| 8599 __extension__ static __inline float32x4x2_t __attribute__ ((__always_inline__)) | 8599 __extension__ static __inline float32x4x2_t __attribute__ ((__always_inline__)) |
| 8600 vld2q_f32 (const float32_t * __a) | 8600 vld2q_f32 (const float32_t * __a) |
| 8601 { | 8601 { |
| 8602 union { float32x4x2_t __i; __builtin_neon_oi __o; } __rv; | 8602 union { float32x4x2_t __i; __builtin_neon_oi __o; } __rv; |
| 8603 __rv.__o = __builtin_neon_vld2v4sf (__a); | 8603 __rv.__o = __builtin_neon_vld2v4sf ((const __builtin_neon_sf *) __a); |
| 8604 return __rv.__i; | 8604 return __rv.__i; |
| 8605 } | 8605 } |
| 8606 | 8606 |
| 8607 __extension__ static __inline uint8x16x2_t __attribute__ ((__always_inline__)) | 8607 __extension__ static __inline uint8x16x2_t __attribute__ ((__always_inline__)) |
| 8608 vld2q_u8 (const uint8_t * __a) | 8608 vld2q_u8 (const uint8_t * __a) |
| 8674 __extension__ static __inline float32x2x2_t __attribute__ ((__always_inline__)) | 8674 __extension__ static __inline float32x2x2_t __attribute__ ((__always_inline__)) |
| 8675 vld2_lane_f32 (const float32_t * __a, float32x2x2_t __b, const int __c) | 8675 vld2_lane_f32 (const float32_t * __a, float32x2x2_t __b, const int __c) |
| 8676 { | 8676 { |
| 8677 union { float32x2x2_t __i; __builtin_neon_ti __o; } __bu = { __b }; | 8677 union { float32x2x2_t __i; __builtin_neon_ti __o; } __bu = { __b }; |
| 8678 union { float32x2x2_t __i; __builtin_neon_ti __o; } __rv; | 8678 union { float32x2x2_t __i; __builtin_neon_ti __o; } __rv; |
| 8679 __rv.__o = __builtin_neon_vld2_lanev2sf (__a, __bu.__o, __c); | 8679 __rv.__o = __builtin_neon_vld2_lanev2sf ((const __builtin_neon_sf *) __a, __bu.__o, __c); |
| 8680 return __rv.__i; | 8680 return __rv.__i; |
| 8681 } | 8681 } |
| 8682 | 8682 |
| 8683 __extension__ static __inline uint8x8x2_t __attribute__ ((__always_inline__)) | 8683 __extension__ static __inline uint8x8x2_t __attribute__ ((__always_inline__)) |
| 8684 vld2_lane_u8 (const uint8_t * __a, uint8x8x2_t __b, const int __c) | 8684 vld2_lane_u8 (const uint8_t * __a, uint8x8x2_t __b, const int __c) |
| 8746 __extension__ static __inline float32x4x2_t __attribute__ ((__always_inline__)) | 8746 __extension__ static __inline float32x4x2_t __attribute__ ((__always_inline__)) |
| 8747 vld2q_lane_f32 (const float32_t * __a, float32x4x2_t __b, const int __c) | 8747 vld2q_lane_f32 (const float32_t * __a, float32x4x2_t __b, const int __c) |
| 8748 { | 8748 { |
| 8749 union { float32x4x2_t __i; __builtin_neon_oi __o; } __bu = { __b }; | 8749 union { float32x4x2_t __i; __builtin_neon_oi __o; } __bu = { __b }; |
| 8750 union { float32x4x2_t __i; __builtin_neon_oi __o; } __rv; | 8750 union { float32x4x2_t __i; __builtin_neon_oi __o; } __rv; |
| 8751 __rv.__o = __builtin_neon_vld2_lanev4sf (__a, __bu.__o, __c); | 8751 __rv.__o = __builtin_neon_vld2_lanev4sf ((const __builtin_neon_sf *) __a, __bu.__o, __c); |
| 8752 return __rv.__i; | 8752 return __rv.__i; |
| 8753 } | 8753 } |
| 8754 | 8754 |
| 8755 __extension__ static __inline uint16x8x2_t __attribute__ ((__always_inline__)) | 8755 __extension__ static __inline uint16x8x2_t __attribute__ ((__always_inline__)) |
| 8756 vld2q_lane_u16 (const uint16_t * __a, uint16x8x2_t __b, const int __c) | 8756 vld2q_lane_u16 (const uint16_t * __a, uint16x8x2_t __b, const int __c) |
| 8805 | 8805 |
| 8806 __extension__ static __inline float32x2x2_t __attribute__ ((__always_inline__)) | 8806 __extension__ static __inline float32x2x2_t __attribute__ ((__always_inline__)) |
| 8807 vld2_dup_f32 (const float32_t * __a) | 8807 vld2_dup_f32 (const float32_t * __a) |
| 8808 { | 8808 { |
| 8809 union { float32x2x2_t __i; __builtin_neon_ti __o; } __rv; | 8809 union { float32x2x2_t __i; __builtin_neon_ti __o; } __rv; |
| 8810 __rv.__o = __builtin_neon_vld2_dupv2sf (__a); | 8810 __rv.__o = __builtin_neon_vld2_dupv2sf ((const __builtin_neon_sf *) __a); |
| 8811 return __rv.__i; | 8811 return __rv.__i; |
| 8812 } | 8812 } |
| 8813 | 8813 |
| 8814 __extension__ static __inline uint8x8x2_t __attribute__ ((__always_inline__)) | 8814 __extension__ static __inline uint8x8x2_t __attribute__ ((__always_inline__)) |
| 8815 vld2_dup_u8 (const uint8_t * __a) | 8815 vld2_dup_u8 (const uint8_t * __a) |
| 8890 | 8890 |
| 8891 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8891 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8892 vst2_f32 (float32_t * __a, float32x2x2_t __b) | 8892 vst2_f32 (float32_t * __a, float32x2x2_t __b) |
| 8893 { | 8893 { |
| 8894 union { float32x2x2_t __i; __builtin_neon_ti __o; } __bu = { __b }; | 8894 union { float32x2x2_t __i; __builtin_neon_ti __o; } __bu = { __b }; |
| 8895 __builtin_neon_vst2v2sf (__a, __bu.__o); | 8895 __builtin_neon_vst2v2sf ((__builtin_neon_sf *) __a, __bu.__o); |
| 8896 } | 8896 } |
| 8897 | 8897 |
| 8898 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8898 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8899 vst2_u8 (uint8_t * __a, uint8x8x2_t __b) | 8899 vst2_u8 (uint8_t * __a, uint8x8x2_t __b) |
| 8900 { | 8900 { |
| 8967 | 8967 |
| 8968 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8968 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8969 vst2q_f32 (float32_t * __a, float32x4x2_t __b) | 8969 vst2q_f32 (float32_t * __a, float32x4x2_t __b) |
| 8970 { | 8970 { |
| 8971 union { float32x4x2_t __i; __builtin_neon_oi __o; } __bu = { __b }; | 8971 union { float32x4x2_t __i; __builtin_neon_oi __o; } __bu = { __b }; |
| 8972 __builtin_neon_vst2v4sf (__a, __bu.__o); | 8972 __builtin_neon_vst2v4sf ((__builtin_neon_sf *) __a, __bu.__o); |
| 8973 } | 8973 } |
| 8974 | 8974 |
| 8975 __extension__ static __inline void __attribute__ ((__always_inline__)) | 8975 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 8976 vst2q_u8 (uint8_t * __a, uint8x16x2_t __b) | 8976 vst2q_u8 (uint8_t * __a, uint8x16x2_t __b) |
| 8977 { | 8977 { |
| 9030 | 9030 |
| 9031 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9031 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9032 vst2_lane_f32 (float32_t * __a, float32x2x2_t __b, const int __c) | 9032 vst2_lane_f32 (float32_t * __a, float32x2x2_t __b, const int __c) |
| 9033 { | 9033 { |
| 9034 union { float32x2x2_t __i; __builtin_neon_ti __o; } __bu = { __b }; | 9034 union { float32x2x2_t __i; __builtin_neon_ti __o; } __bu = { __b }; |
| 9035 __builtin_neon_vst2_lanev2sf (__a, __bu.__o, __c); | 9035 __builtin_neon_vst2_lanev2sf ((__builtin_neon_sf *) __a, __bu.__o, __c); |
| 9036 } | 9036 } |
| 9037 | 9037 |
| 9038 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9038 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9039 vst2_lane_u8 (uint8_t * __a, uint8x8x2_t __b, const int __c) | 9039 vst2_lane_u8 (uint8_t * __a, uint8x8x2_t __b, const int __c) |
| 9040 { | 9040 { |
| 9086 | 9086 |
| 9087 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9087 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9088 vst2q_lane_f32 (float32_t * __a, float32x4x2_t __b, const int __c) | 9088 vst2q_lane_f32 (float32_t * __a, float32x4x2_t __b, const int __c) |
| 9089 { | 9089 { |
| 9090 union { float32x4x2_t __i; __builtin_neon_oi __o; } __bu = { __b }; | 9090 union { float32x4x2_t __i; __builtin_neon_oi __o; } __bu = { __b }; |
| 9091 __builtin_neon_vst2_lanev4sf (__a, __bu.__o, __c); | 9091 __builtin_neon_vst2_lanev4sf ((__builtin_neon_sf *) __a, __bu.__o, __c); |
| 9092 } | 9092 } |
| 9093 | 9093 |
| 9094 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9094 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9095 vst2q_lane_u16 (uint16_t * __a, uint16x8x2_t __b, const int __c) | 9095 vst2q_lane_u16 (uint16_t * __a, uint16x8x2_t __b, const int __c) |
| 9096 { | 9096 { |
| 9138 | 9138 |
| 9139 __extension__ static __inline float32x2x3_t __attribute__ ((__always_inline__)) | 9139 __extension__ static __inline float32x2x3_t __attribute__ ((__always_inline__)) |
| 9140 vld3_f32 (const float32_t * __a) | 9140 vld3_f32 (const float32_t * __a) |
| 9141 { | 9141 { |
| 9142 union { float32x2x3_t __i; __builtin_neon_ei __o; } __rv; | 9142 union { float32x2x3_t __i; __builtin_neon_ei __o; } __rv; |
| 9143 __rv.__o = __builtin_neon_vld3v2sf (__a); | 9143 __rv.__o = __builtin_neon_vld3v2sf ((const __builtin_neon_sf *) __a); |
| 9144 return __rv.__i; | 9144 return __rv.__i; |
| 9145 } | 9145 } |
| 9146 | 9146 |
| 9147 __extension__ static __inline uint8x8x3_t __attribute__ ((__always_inline__)) | 9147 __extension__ static __inline uint8x8x3_t __attribute__ ((__always_inline__)) |
| 9148 vld3_u8 (const uint8_t * __a) | 9148 vld3_u8 (const uint8_t * __a) |
| 9226 | 9226 |
| 9227 __extension__ static __inline float32x4x3_t __attribute__ ((__always_inline__)) | 9227 __extension__ static __inline float32x4x3_t __attribute__ ((__always_inline__)) |
| 9228 vld3q_f32 (const float32_t * __a) | 9228 vld3q_f32 (const float32_t * __a) |
| 9229 { | 9229 { |
| 9230 union { float32x4x3_t __i; __builtin_neon_ci __o; } __rv; | 9230 union { float32x4x3_t __i; __builtin_neon_ci __o; } __rv; |
| 9231 __rv.__o = __builtin_neon_vld3v4sf (__a); | 9231 __rv.__o = __builtin_neon_vld3v4sf ((const __builtin_neon_sf *) __a); |
| 9232 return __rv.__i; | 9232 return __rv.__i; |
| 9233 } | 9233 } |
| 9234 | 9234 |
| 9235 __extension__ static __inline uint8x16x3_t __attribute__ ((__always_inline__)) | 9235 __extension__ static __inline uint8x16x3_t __attribute__ ((__always_inline__)) |
| 9236 vld3q_u8 (const uint8_t * __a) | 9236 vld3q_u8 (const uint8_t * __a) |
| 9302 __extension__ static __inline float32x2x3_t __attribute__ ((__always_inline__)) | 9302 __extension__ static __inline float32x2x3_t __attribute__ ((__always_inline__)) |
| 9303 vld3_lane_f32 (const float32_t * __a, float32x2x3_t __b, const int __c) | 9303 vld3_lane_f32 (const float32_t * __a, float32x2x3_t __b, const int __c) |
| 9304 { | 9304 { |
| 9305 union { float32x2x3_t __i; __builtin_neon_ei __o; } __bu = { __b }; | 9305 union { float32x2x3_t __i; __builtin_neon_ei __o; } __bu = { __b }; |
| 9306 union { float32x2x3_t __i; __builtin_neon_ei __o; } __rv; | 9306 union { float32x2x3_t __i; __builtin_neon_ei __o; } __rv; |
| 9307 __rv.__o = __builtin_neon_vld3_lanev2sf (__a, __bu.__o, __c); | 9307 __rv.__o = __builtin_neon_vld3_lanev2sf ((const __builtin_neon_sf *) __a, __bu.__o, __c); |
| 9308 return __rv.__i; | 9308 return __rv.__i; |
| 9309 } | 9309 } |
| 9310 | 9310 |
| 9311 __extension__ static __inline uint8x8x3_t __attribute__ ((__always_inline__)) | 9311 __extension__ static __inline uint8x8x3_t __attribute__ ((__always_inline__)) |
| 9312 vld3_lane_u8 (const uint8_t * __a, uint8x8x3_t __b, const int __c) | 9312 vld3_lane_u8 (const uint8_t * __a, uint8x8x3_t __b, const int __c) |
| 9374 __extension__ static __inline float32x4x3_t __attribute__ ((__always_inline__)) | 9374 __extension__ static __inline float32x4x3_t __attribute__ ((__always_inline__)) |
| 9375 vld3q_lane_f32 (const float32_t * __a, float32x4x3_t __b, const int __c) | 9375 vld3q_lane_f32 (const float32_t * __a, float32x4x3_t __b, const int __c) |
| 9376 { | 9376 { |
| 9377 union { float32x4x3_t __i; __builtin_neon_ci __o; } __bu = { __b }; | 9377 union { float32x4x3_t __i; __builtin_neon_ci __o; } __bu = { __b }; |
| 9378 union { float32x4x3_t __i; __builtin_neon_ci __o; } __rv; | 9378 union { float32x4x3_t __i; __builtin_neon_ci __o; } __rv; |
| 9379 __rv.__o = __builtin_neon_vld3_lanev4sf (__a, __bu.__o, __c); | 9379 __rv.__o = __builtin_neon_vld3_lanev4sf ((const __builtin_neon_sf *) __a, __bu.__o, __c); |
| 9380 return __rv.__i; | 9380 return __rv.__i; |
| 9381 } | 9381 } |
| 9382 | 9382 |
| 9383 __extension__ static __inline uint16x8x3_t __attribute__ ((__always_inline__)) | 9383 __extension__ static __inline uint16x8x3_t __attribute__ ((__always_inline__)) |
| 9384 vld3q_lane_u16 (const uint16_t * __a, uint16x8x3_t __b, const int __c) | 9384 vld3q_lane_u16 (const uint16_t * __a, uint16x8x3_t __b, const int __c) |
| 9433 | 9433 |
| 9434 __extension__ static __inline float32x2x3_t __attribute__ ((__always_inline__)) | 9434 __extension__ static __inline float32x2x3_t __attribute__ ((__always_inline__)) |
| 9435 vld3_dup_f32 (const float32_t * __a) | 9435 vld3_dup_f32 (const float32_t * __a) |
| 9436 { | 9436 { |
| 9437 union { float32x2x3_t __i; __builtin_neon_ei __o; } __rv; | 9437 union { float32x2x3_t __i; __builtin_neon_ei __o; } __rv; |
| 9438 __rv.__o = __builtin_neon_vld3_dupv2sf (__a); | 9438 __rv.__o = __builtin_neon_vld3_dupv2sf ((const __builtin_neon_sf *) __a); |
| 9439 return __rv.__i; | 9439 return __rv.__i; |
| 9440 } | 9440 } |
| 9441 | 9441 |
| 9442 __extension__ static __inline uint8x8x3_t __attribute__ ((__always_inline__)) | 9442 __extension__ static __inline uint8x8x3_t __attribute__ ((__always_inline__)) |
| 9443 vld3_dup_u8 (const uint8_t * __a) | 9443 vld3_dup_u8 (const uint8_t * __a) |
| 9518 | 9518 |
| 9519 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9519 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9520 vst3_f32 (float32_t * __a, float32x2x3_t __b) | 9520 vst3_f32 (float32_t * __a, float32x2x3_t __b) |
| 9521 { | 9521 { |
| 9522 union { float32x2x3_t __i; __builtin_neon_ei __o; } __bu = { __b }; | 9522 union { float32x2x3_t __i; __builtin_neon_ei __o; } __bu = { __b }; |
| 9523 __builtin_neon_vst3v2sf (__a, __bu.__o); | 9523 __builtin_neon_vst3v2sf ((__builtin_neon_sf *) __a, __bu.__o); |
| 9524 } | 9524 } |
| 9525 | 9525 |
| 9526 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9526 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9527 vst3_u8 (uint8_t * __a, uint8x8x3_t __b) | 9527 vst3_u8 (uint8_t * __a, uint8x8x3_t __b) |
| 9528 { | 9528 { |
| 9595 | 9595 |
| 9596 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9596 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9597 vst3q_f32 (float32_t * __a, float32x4x3_t __b) | 9597 vst3q_f32 (float32_t * __a, float32x4x3_t __b) |
| 9598 { | 9598 { |
| 9599 union { float32x4x3_t __i; __builtin_neon_ci __o; } __bu = { __b }; | 9599 union { float32x4x3_t __i; __builtin_neon_ci __o; } __bu = { __b }; |
| 9600 __builtin_neon_vst3v4sf (__a, __bu.__o); | 9600 __builtin_neon_vst3v4sf ((__builtin_neon_sf *) __a, __bu.__o); |
| 9601 } | 9601 } |
| 9602 | 9602 |
| 9603 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9603 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9604 vst3q_u8 (uint8_t * __a, uint8x16x3_t __b) | 9604 vst3q_u8 (uint8_t * __a, uint8x16x3_t __b) |
| 9605 { | 9605 { |
| 9658 | 9658 |
| 9659 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9659 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9660 vst3_lane_f32 (float32_t * __a, float32x2x3_t __b, const int __c) | 9660 vst3_lane_f32 (float32_t * __a, float32x2x3_t __b, const int __c) |
| 9661 { | 9661 { |
| 9662 union { float32x2x3_t __i; __builtin_neon_ei __o; } __bu = { __b }; | 9662 union { float32x2x3_t __i; __builtin_neon_ei __o; } __bu = { __b }; |
| 9663 __builtin_neon_vst3_lanev2sf (__a, __bu.__o, __c); | 9663 __builtin_neon_vst3_lanev2sf ((__builtin_neon_sf *) __a, __bu.__o, __c); |
| 9664 } | 9664 } |
| 9665 | 9665 |
| 9666 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9666 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9667 vst3_lane_u8 (uint8_t * __a, uint8x8x3_t __b, const int __c) | 9667 vst3_lane_u8 (uint8_t * __a, uint8x8x3_t __b, const int __c) |
| 9668 { | 9668 { |
| 9714 | 9714 |
| 9715 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9715 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9716 vst3q_lane_f32 (float32_t * __a, float32x4x3_t __b, const int __c) | 9716 vst3q_lane_f32 (float32_t * __a, float32x4x3_t __b, const int __c) |
| 9717 { | 9717 { |
| 9718 union { float32x4x3_t __i; __builtin_neon_ci __o; } __bu = { __b }; | 9718 union { float32x4x3_t __i; __builtin_neon_ci __o; } __bu = { __b }; |
| 9719 __builtin_neon_vst3_lanev4sf (__a, __bu.__o, __c); | 9719 __builtin_neon_vst3_lanev4sf ((__builtin_neon_sf *) __a, __bu.__o, __c); |
| 9720 } | 9720 } |
| 9721 | 9721 |
| 9722 __extension__ static __inline void __attribute__ ((__always_inline__)) | 9722 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 9723 vst3q_lane_u16 (uint16_t * __a, uint16x8x3_t __b, const int __c) | 9723 vst3q_lane_u16 (uint16_t * __a, uint16x8x3_t __b, const int __c) |
| 9724 { | 9724 { |
| 9766 | 9766 |
| 9767 __extension__ static __inline float32x2x4_t __attribute__ ((__always_inline__)) | 9767 __extension__ static __inline float32x2x4_t __attribute__ ((__always_inline__)) |
| 9768 vld4_f32 (const float32_t * __a) | 9768 vld4_f32 (const float32_t * __a) |
| 9769 { | 9769 { |
| 9770 union { float32x2x4_t __i; __builtin_neon_oi __o; } __rv; | 9770 union { float32x2x4_t __i; __builtin_neon_oi __o; } __rv; |
| 9771 __rv.__o = __builtin_neon_vld4v2sf (__a); | 9771 __rv.__o = __builtin_neon_vld4v2sf ((const __builtin_neon_sf *) __a); |
| 9772 return __rv.__i; | 9772 return __rv.__i; |
| 9773 } | 9773 } |
| 9774 | 9774 |
| 9775 __extension__ static __inline uint8x8x4_t __attribute__ ((__always_inline__)) | 9775 __extension__ static __inline uint8x8x4_t __attribute__ ((__always_inline__)) |
| 9776 vld4_u8 (const uint8_t * __a) | 9776 vld4_u8 (const uint8_t * __a) |
| 9854 | 9854 |
| 9855 __extension__ static __inline float32x4x4_t __attribute__ ((__always_inline__)) | 9855 __extension__ static __inline float32x4x4_t __attribute__ ((__always_inline__)) |
| 9856 vld4q_f32 (const float32_t * __a) | 9856 vld4q_f32 (const float32_t * __a) |
| 9857 { | 9857 { |
| 9858 union { float32x4x4_t __i; __builtin_neon_xi __o; } __rv; | 9858 union { float32x4x4_t __i; __builtin_neon_xi __o; } __rv; |
| 9859 __rv.__o = __builtin_neon_vld4v4sf (__a); | 9859 __rv.__o = __builtin_neon_vld4v4sf ((const __builtin_neon_sf *) __a); |
| 9860 return __rv.__i; | 9860 return __rv.__i; |
| 9861 } | 9861 } |
| 9862 | 9862 |
| 9863 __extension__ static __inline uint8x16x4_t __attribute__ ((__always_inline__)) | 9863 __extension__ static __inline uint8x16x4_t __attribute__ ((__always_inline__)) |
| 9864 vld4q_u8 (const uint8_t * __a) | 9864 vld4q_u8 (const uint8_t * __a) |
| 9930 __extension__ static __inline float32x2x4_t __attribute__ ((__always_inline__)) | 9930 __extension__ static __inline float32x2x4_t __attribute__ ((__always_inline__)) |
| 9931 vld4_lane_f32 (const float32_t * __a, float32x2x4_t __b, const int __c) | 9931 vld4_lane_f32 (const float32_t * __a, float32x2x4_t __b, const int __c) |
| 9932 { | 9932 { |
| 9933 union { float32x2x4_t __i; __builtin_neon_oi __o; } __bu = { __b }; | 9933 union { float32x2x4_t __i; __builtin_neon_oi __o; } __bu = { __b }; |
| 9934 union { float32x2x4_t __i; __builtin_neon_oi __o; } __rv; | 9934 union { float32x2x4_t __i; __builtin_neon_oi __o; } __rv; |
| 9935 __rv.__o = __builtin_neon_vld4_lanev2sf (__a, __bu.__o, __c); | 9935 __rv.__o = __builtin_neon_vld4_lanev2sf ((const __builtin_neon_sf *) __a, __bu.__o, __c); |
| 9936 return __rv.__i; | 9936 return __rv.__i; |
| 9937 } | 9937 } |
| 9938 | 9938 |
| 9939 __extension__ static __inline uint8x8x4_t __attribute__ ((__always_inline__)) | 9939 __extension__ static __inline uint8x8x4_t __attribute__ ((__always_inline__)) |
| 9940 vld4_lane_u8 (const uint8_t * __a, uint8x8x4_t __b, const int __c) | 9940 vld4_lane_u8 (const uint8_t * __a, uint8x8x4_t __b, const int __c) |
| 10002 __extension__ static __inline float32x4x4_t __attribute__ ((__always_inline__)) | 10002 __extension__ static __inline float32x4x4_t __attribute__ ((__always_inline__)) |
| 10003 vld4q_lane_f32 (const float32_t * __a, float32x4x4_t __b, const int __c) | 10003 vld4q_lane_f32 (const float32_t * __a, float32x4x4_t __b, const int __c) |
| 10004 { | 10004 { |
| 10005 union { float32x4x4_t __i; __builtin_neon_xi __o; } __bu = { __b }; | 10005 union { float32x4x4_t __i; __builtin_neon_xi __o; } __bu = { __b }; |
| 10006 union { float32x4x4_t __i; __builtin_neon_xi __o; } __rv; | 10006 union { float32x4x4_t __i; __builtin_neon_xi __o; } __rv; |
| 10007 __rv.__o = __builtin_neon_vld4_lanev4sf (__a, __bu.__o, __c); | 10007 __rv.__o = __builtin_neon_vld4_lanev4sf ((const __builtin_neon_sf *) __a, __bu.__o, __c); |
| 10008 return __rv.__i; | 10008 return __rv.__i; |
| 10009 } | 10009 } |
| 10010 | 10010 |
| 10011 __extension__ static __inline uint16x8x4_t __attribute__ ((__always_inline__)) | 10011 __extension__ static __inline uint16x8x4_t __attribute__ ((__always_inline__)) |
| 10012 vld4q_lane_u16 (const uint16_t * __a, uint16x8x4_t __b, const int __c) | 10012 vld4q_lane_u16 (const uint16_t * __a, uint16x8x4_t __b, const int __c) |
| 10061 | 10061 |
| 10062 __extension__ static __inline float32x2x4_t __attribute__ ((__always_inline__)) | 10062 __extension__ static __inline float32x2x4_t __attribute__ ((__always_inline__)) |
| 10063 vld4_dup_f32 (const float32_t * __a) | 10063 vld4_dup_f32 (const float32_t * __a) |
| 10064 { | 10064 { |
| 10065 union { float32x2x4_t __i; __builtin_neon_oi __o; } __rv; | 10065 union { float32x2x4_t __i; __builtin_neon_oi __o; } __rv; |
| 10066 __rv.__o = __builtin_neon_vld4_dupv2sf (__a); | 10066 __rv.__o = __builtin_neon_vld4_dupv2sf ((const __builtin_neon_sf *) __a); |
| 10067 return __rv.__i; | 10067 return __rv.__i; |
| 10068 } | 10068 } |
| 10069 | 10069 |
| 10070 __extension__ static __inline uint8x8x4_t __attribute__ ((__always_inline__)) | 10070 __extension__ static __inline uint8x8x4_t __attribute__ ((__always_inline__)) |
| 10071 vld4_dup_u8 (const uint8_t * __a) | 10071 vld4_dup_u8 (const uint8_t * __a) |
| 10146 | 10146 |
| 10147 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10147 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10148 vst4_f32 (float32_t * __a, float32x2x4_t __b) | 10148 vst4_f32 (float32_t * __a, float32x2x4_t __b) |
| 10149 { | 10149 { |
| 10150 union { float32x2x4_t __i; __builtin_neon_oi __o; } __bu = { __b }; | 10150 union { float32x2x4_t __i; __builtin_neon_oi __o; } __bu = { __b }; |
| 10151 __builtin_neon_vst4v2sf (__a, __bu.__o); | 10151 __builtin_neon_vst4v2sf ((__builtin_neon_sf *) __a, __bu.__o); |
| 10152 } | 10152 } |
| 10153 | 10153 |
| 10154 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10154 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10155 vst4_u8 (uint8_t * __a, uint8x8x4_t __b) | 10155 vst4_u8 (uint8_t * __a, uint8x8x4_t __b) |
| 10156 { | 10156 { |
| 10223 | 10223 |
| 10224 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10224 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10225 vst4q_f32 (float32_t * __a, float32x4x4_t __b) | 10225 vst4q_f32 (float32_t * __a, float32x4x4_t __b) |
| 10226 { | 10226 { |
| 10227 union { float32x4x4_t __i; __builtin_neon_xi __o; } __bu = { __b }; | 10227 union { float32x4x4_t __i; __builtin_neon_xi __o; } __bu = { __b }; |
| 10228 __builtin_neon_vst4v4sf (__a, __bu.__o); | 10228 __builtin_neon_vst4v4sf ((__builtin_neon_sf *) __a, __bu.__o); |
| 10229 } | 10229 } |
| 10230 | 10230 |
| 10231 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10231 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10232 vst4q_u8 (uint8_t * __a, uint8x16x4_t __b) | 10232 vst4q_u8 (uint8_t * __a, uint8x16x4_t __b) |
| 10233 { | 10233 { |
| 10286 | 10286 |
| 10287 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10287 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10288 vst4_lane_f32 (float32_t * __a, float32x2x4_t __b, const int __c) | 10288 vst4_lane_f32 (float32_t * __a, float32x2x4_t __b, const int __c) |
| 10289 { | 10289 { |
| 10290 union { float32x2x4_t __i; __builtin_neon_oi __o; } __bu = { __b }; | 10290 union { float32x2x4_t __i; __builtin_neon_oi __o; } __bu = { __b }; |
| 10291 __builtin_neon_vst4_lanev2sf (__a, __bu.__o, __c); | 10291 __builtin_neon_vst4_lanev2sf ((__builtin_neon_sf *) __a, __bu.__o, __c); |
| 10292 } | 10292 } |
| 10293 | 10293 |
| 10294 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10294 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10295 vst4_lane_u8 (uint8_t * __a, uint8x8x4_t __b, const int __c) | 10295 vst4_lane_u8 (uint8_t * __a, uint8x8x4_t __b, const int __c) |
| 10296 { | 10296 { |
| 10342 | 10342 |
| 10343 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10343 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10344 vst4q_lane_f32 (float32_t * __a, float32x4x4_t __b, const int __c) | 10344 vst4q_lane_f32 (float32_t * __a, float32x4x4_t __b, const int __c) |
| 10345 { | 10345 { |
| 10346 union { float32x4x4_t __i; __builtin_neon_xi __o; } __bu = { __b }; | 10346 union { float32x4x4_t __i; __builtin_neon_xi __o; } __bu = { __b }; |
| 10347 __builtin_neon_vst4_lanev4sf (__a, __bu.__o, __c); | 10347 __builtin_neon_vst4_lanev4sf ((__builtin_neon_sf *) __a, __bu.__o, __c); |
| 10348 } | 10348 } |
| 10349 | 10349 |
| 10350 __extension__ static __inline void __attribute__ ((__always_inline__)) | 10350 __extension__ static __inline void __attribute__ ((__always_inline__)) |
| 10351 vst4q_lane_u16 (uint16_t * __a, uint16x8x4_t __b, const int __c) | 10351 vst4q_lane_u16 (uint16_t * __a, uint16x8x4_t __b, const int __c) |
| 10352 { | 10352 { |