1 /* 2 * Copyright (C) 2012 University of Szeged 3 * Copyright (C) 2012 Gabor Rapcsanyi 4 * 5 * Redistribution and use in source and binary forms, with or without 6 * modification, are permitted provided that the following conditions 7 * are met: 8 * 1. Redistributions of source code must retain the above copyright 9 * notice, this list of conditions and the following disclaimer. 10 * 2. Redistributions in binary form must reproduce the above copyright 11 * notice, this list of conditions and the following disclaimer in the 12 * documentation and/or other materials provided with the distribution. 13 * 14 * THIS SOFTWARE IS PROVIDED BY UNIVERSITY OF SZEGED ``AS IS'' AND ANY 15 * EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT LIMITED TO, THE 16 * IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR A PARTICULAR 17 * PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL UNIVERSITY OF SZEGED OR 18 * CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL, SPECIAL, 19 * EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT LIMITED TO, 20 * PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE, DATA, OR 21 * PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY THEORY 22 * OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT 23 * (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE 24 * OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE. 25 */ 26 27 #ifndef NEONHelpers_h 28 #define NEONHelpers_h 29 30 #if HAVE(ARM_NEON_INTRINSICS) 31 32 #include <arm_neon.h> 33 34 namespace WebCore { 35 36 inline float32x4_t loadRGBA8AsFloat(uint32_t* source) 37 { 38 uint32x2_t temporary1 = {0, 0}; 39 temporary1 = vset_lane_u32(*source, temporary1, 0); 40 uint16x4_t temporary2 = vget_low_u16(vmovl_u8(vreinterpret_u8_u32(temporary1))); 41 return vcvtq_f32_u32(vmovl_u16(temporary2)); 42 } 43 44 inline void storeFloatAsRGBA8(float32x4_t data, uint32_t* destination) 45 { 46 uint16x4_t temporary1 = vmovn_u32(vcvtq_u32_f32(data)); 47 uint8x8_t temporary2 = vmovn_u16(vcombine_u16(temporary1, temporary1)); 48 *destination = vget_lane_u32(vreinterpret_u32_u8(temporary2), 0); 49 } 50 51 } // namespace WebCore 52 53 #endif // HAVE(ARM_NEON_INTRINSICS) 54 55 #endif // NEONHelpers_h 56
