27 #include <rte_thash_gfni.h> 29 #if defined(RTE_ARCH_X86) || defined(__ARM_NEON) 37 static const __m128i rte_thash_ipv6_bswap_mask = {
38 0x0405060700010203ULL, 0x0C0D0E0F08090A0BULL};
45 #define RTE_THASH_V4_L3_LEN ((sizeof(struct rte_ipv4_tuple) - \ 46 sizeof(((struct rte_ipv4_tuple *)0)->sctp_tag)) / 4) 53 #define RTE_THASH_V4_L4_LEN ((sizeof(struct rte_ipv4_tuple)) / 4) 59 #define RTE_THASH_V6_L3_LEN ((sizeof(struct rte_ipv6_tuple) - \ 60 sizeof(((struct rte_ipv6_tuple *)0)->sctp_tag)) / 4) 67 #define RTE_THASH_V6_L4_LEN ((sizeof(struct rte_ipv6_tuple)) / 4) 103 union __rte_aligned(XMM_SIZE) rte_thash_tuple {
105 union rte_thash_tuple {
125 for (i = 0; i < (len >> 2); i++)
139 union rte_thash_tuple *targ)
142 __m128i ipv6 = _mm_loadu_si128((
const __m128i *)orig->
src_addr);
143 *(__m128i *)targ->v6.src_addr =
144 _mm_shuffle_epi8(ipv6, rte_thash_ipv6_bswap_mask);
145 ipv6 = _mm_loadu_si128((
const __m128i *)orig->
dst_addr);
146 *(__m128i *)targ->v6.dst_addr =
147 _mm_shuffle_epi8(ipv6, rte_thash_ipv6_bswap_mask);
148 #elif defined(__ARM_NEON) 149 uint8x16_t ipv6 = vld1q_u8((uint8_t
const *)orig->
src_addr);
150 vst1q_u8((uint8_t *)targ->v6.src_addr, vrev32q_u8(ipv6));
151 ipv6 = vld1q_u8((uint8_t
const *)orig->
dst_addr);
152 vst1q_u8((uint8_t *)targ->v6.dst_addr, vrev32q_u8(ipv6));
155 for (i = 0; i < 4; i++) {
156 *((uint32_t *)targ->v6.src_addr + i) =
158 *((uint32_t *)targ->v6.dst_addr + i) =
175 static inline uint32_t
177 const uint8_t *rss_key)
179 uint32_t i, j, map, ret = 0;
181 for (j = 0; j < input_len; j++) {
182 for (map = input_tuple[j]; map; map &= (map - 1)) {
185 (uint32_t)((uint64_t)(
rte_cpu_to_be_32(((
const uint32_t *)rss_key)[j + 1])) >>
205 static inline uint32_t
207 const uint8_t *rss_key)
209 uint32_t i, j, map, ret = 0;
211 for (j = 0; j < input_len; j++) {
212 for (map = input_tuple[j]; map; map &= (map - 1)) {
214 ret ^= ((
const uint32_t *)rss_key)[j] << (31 - i) |
215 (uint32_t)((uint64_t)(((
const uint32_t *)rss_key)[j + 1]) >> (i + 1));
248 #define RTE_THASH_RETA_SZ_MIN 2U 250 #define RTE_THASH_RETA_SZ_MAX 16U 256 #define RTE_THASH_IGNORE_PERIOD_OVERFLOW 0x1 261 #define RTE_THASH_MINIMAL_SEQ 0x2 264 struct rte_thash_ctx;
266 struct rte_thash_subtuple_helper;
290 struct rte_thash_ctx *
292 uint8_t *key, uint32_t flags);
304 struct rte_thash_ctx *
349 struct rte_thash_subtuple_helper *
369 uint32_t hash, uint32_t desired_hash);
445 struct rte_thash_subtuple_helper *h,
446 uint8_t *tuple,
unsigned int tuple_len,
447 uint32_t desired_value,
unsigned int attempts,
int rte_thash_add_helper(struct rte_thash_ctx *ctx, const char *name, uint32_t len, uint32_t offset)
int(* rte_thash_check_tuple_t)(void *userdata, uint8_t *tuple)
int rte_thash_gfni_supported(void)
const uint64_t * rte_thash_get_gfni_matrices(struct rte_thash_ctx *ctx)
static rte_be32_t rte_cpu_to_be_32(uint32_t x)
static uint32_t rte_bsf32(uint32_t v)
static void rte_convert_rss_key(const uint32_t *orig, uint32_t *targ, int len)
uint32_t rte_thash_get_complement(struct rte_thash_subtuple_helper *h, uint32_t hash, uint32_t desired_hash)
static void rte_thash_load_v6_addrs(const struct rte_ipv6_hdr *orig, union rte_thash_tuple *targ)
static uint32_t rte_softrss(uint32_t *input_tuple, uint32_t input_len, const uint8_t *rss_key)
void rte_thash_complete_matrix(uint64_t *matrixes, const uint8_t *rss_key, int size)
void rte_thash_free_ctx(struct rte_thash_ctx *ctx)
struct rte_thash_subtuple_helper * rte_thash_get_helper(struct rte_thash_ctx *ctx, const char *name)
int rte_thash_adjust_tuple(struct rte_thash_ctx *ctx, struct rte_thash_subtuple_helper *h, uint8_t *tuple, unsigned int tuple_len, uint32_t desired_value, unsigned int attempts, rte_thash_check_tuple_t fn, void *userdata)
struct rte_thash_ctx * rte_thash_init_ctx(const char *name, uint32_t key_len, uint32_t reta_sz, uint8_t *key, uint32_t flags)
struct rte_thash_ctx * rte_thash_find_existing(const char *name)
static uint32_t rte_be_to_cpu_32(rte_be32_t x)
static uint32_t rte_softrss_be(uint32_t *input_tuple, uint32_t input_len, const uint8_t *rss_key)
const uint8_t * rte_thash_get_key(struct rte_thash_ctx *ctx)