lib/librte_eal/common/include/arch/arm/rte_vect.h

   1 /*-
   2  *   BSD LICENSE
   3  *
   4  *   Copyright(c) 2015 Cavium Networks. All rights reserved.
   5  *
   6  *   Redistribution and use in source and binary forms, with or without
   7  *   modification, are permitted provided that the following conditions
   8  *   are met:
   9  *
  10  *     * Redistributions of source code must retain the above copyright
  11  *       notice, this list of conditions and the following disclaimer.
  12  *     * Redistributions in binary form must reproduce the above copyright
  13  *       notice, this list of conditions and the following disclaimer in
  14  *       the documentation and/or other materials provided with the
  15  *       distribution.
  16  *     * Neither the name of Cavium Networks nor the names of its
  17  *       contributors may be used to endorse or promote products derived
  18  *       from this software without specific prior written permission.
  19  *
  20  *   THIS SOFTWARE IS PROVIDED BY THE COPYRIGHT HOLDERS AND CONTRIBUTORS
  21  *   "AS IS" AND ANY EXPRESS OR IMPLIED WARRANTIES, INCLUDING, BUT NOT
  22  *   LIMITED TO, THE IMPLIED WARRANTIES OF MERCHANTABILITY AND FITNESS FOR
  23  *   A PARTICULAR PURPOSE ARE DISCLAIMED. IN NO EVENT SHALL THE COPYRIGHT
  24  *   OWNER OR CONTRIBUTORS BE LIABLE FOR ANY DIRECT, INDIRECT, INCIDENTAL,
  25  *   SPECIAL, EXEMPLARY, OR CONSEQUENTIAL DAMAGES (INCLUDING, BUT NOT
  26  *   LIMITED TO, PROCUREMENT OF SUBSTITUTE GOODS OR SERVICES; LOSS OF USE,
  27  *   DATA, OR PROFITS; OR BUSINESS INTERRUPTION) HOWEVER CAUSED AND ON ANY
  28  *   THEORY OF LIABILITY, WHETHER IN CONTRACT, STRICT LIABILITY, OR TORT
  29  *   (INCLUDING NEGLIGENCE OR OTHERWISE) ARISING IN ANY WAY OUT OF THE USE
  30  *   OF THIS SOFTWARE, EVEN IF ADVISED OF THE POSSIBILITY OF SUCH DAMAGE.
  31  */
  32
  33 #ifndef _RTE_VECT_ARM_H_
  34 #define _RTE_VECT_ARM_H_
  35
  36 #include <stdint.h>
  37 #include "arm_neon.h"
  38
  39 #ifdef __cplusplus
  40 extern "C" {
  41 #endif
  42
  43 typedef int32x4_t xmm_t;
  44
  45 #define XMM_SIZE        (sizeof(xmm_t))
  46 #define XMM_MASK        (XMM_SIZE - 1)
  47
  48 typedef union rte_xmm {
  49         xmm_t    x;
  50         uint8_t  u8[XMM_SIZE / sizeof(uint8_t)];
  51         uint16_t u16[XMM_SIZE / sizeof(uint16_t)];
  52         uint32_t u32[XMM_SIZE / sizeof(uint32_t)];
  53         uint64_t u64[XMM_SIZE / sizeof(uint64_t)];
  54         double   pd[XMM_SIZE / sizeof(double)];
  55 } __attribute__((aligned(16))) rte_xmm_t;
  56
  57 #ifdef RTE_ARCH_ARM
  58 /* NEON intrinsic vqtbl1q_u8() is not supported in ARMv7-A(AArch32) */
  59 static __inline uint8x16_t
  60 vqtbl1q_u8(uint8x16_t a, uint8x16_t b)
  61 {
  62         uint8_t i, pos;
  63         rte_xmm_t rte_a, rte_b, rte_ret;
  64
  65         vst1q_u8(rte_a.u8, a);
  66         vst1q_u8(rte_b.u8, b);
  67
  68         for (i = 0; i < 16; i++) {
  69                 pos = rte_b.u8[i];
  70                 if (pos < 16)
  71                         rte_ret.u8[i] = rte_a.u8[pos];
  72                 else
  73                         rte_ret.u8[i] = 0;
  74         }
  75
  76         return vld1q_u8(rte_ret.u8);
  77 }
  78 #endif
  79
  80 #ifdef __cplusplus
  81 }
  82 #endif
  83
  84 #endif