Home
last modified time | relevance | path

Searched refs:ips (Results 1 – 22 of 22) sorted by relevance

/dpdk/lib/fib/
H A Ddir24_8.h123 ips[i + prefetch_offset], nh_sz)); \
124 tmp = ((type *)dp->tbl24)[ips[i] >> 8]; \
131 tmp = ((type *)dp->tbl24)[ips[i] >> 8]; \
157 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk()
159 tmp = get_tbl8(dp, tmp, ips[i], nh_sz); in dir24_8_lookup_bulk()
164 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk()
166 tmp = get_tbl8(dp, tmp, ips[i], nh_sz); in dir24_8_lookup_bulk()
223 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk_uni()
225 tmp = get_tbl8(dp, tmp, ips[i], nh_sz); in dir24_8_lookup_bulk_uni()
230 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk_uni()
[all …]
H A Ddir24_8_avx512.c12 dir24_8_vec_lookup_x16(void *p, const uint32_t *ips, in dir24_8_vec_lookup_x16() argument
30 ip_vec = _mm512_loadu_si512(ips); in dir24_8_vec_lookup_x16()
80 dir24_8_vec_lookup_x8_8b(void *p, const uint32_t *ips, in dir24_8_vec_lookup_x8_8b() argument
91 ip_vec = _mm256_loadu_si256((const void *)ips); in dir24_8_vec_lookup_x8_8b()
118 rte_dir24_8_vec_lookup_bulk_1b(void *p, const uint32_t *ips, in rte_dir24_8_vec_lookup_bulk_1b() argument
126 dir24_8_lookup_bulk_1b(p, ips + i * 16, next_hops + i * 16, in rte_dir24_8_vec_lookup_bulk_1b()
131 rte_dir24_8_vec_lookup_bulk_2b(void *p, const uint32_t *ips, in rte_dir24_8_vec_lookup_bulk_2b() argument
139 dir24_8_lookup_bulk_2b(p, ips + i * 16, next_hops + i * 16, in rte_dir24_8_vec_lookup_bulk_2b()
144 rte_dir24_8_vec_lookup_bulk_4b(void *p, const uint32_t *ips, in rte_dir24_8_vec_lookup_bulk_4b() argument
152 dir24_8_lookup_bulk_4b(p, ips + i * 16, next_hops + i * 16, in rte_dir24_8_vec_lookup_bulk_4b()
[all …]
H A Dtrie_avx512.c12 transpose_x16(uint8_t ips[16][RTE_FIB6_IPV6_ADDR_SIZE], in transpose_x16()
24 tmp1 = _mm512_loadu_si512(&ips[0][0]); in transpose_x16()
25 tmp2 = _mm512_loadu_si512(&ips[4][0]); in transpose_x16()
26 tmp3 = _mm512_loadu_si512(&ips[8][0]); in transpose_x16()
27 tmp4 = _mm512_loadu_si512(&ips[12][0]); in transpose_x16()
51 transpose_x8(uint8_t ips[8][RTE_FIB6_IPV6_ADDR_SIZE], in transpose_x8()
60 tmp1 = _mm512_loadu_si512(&ips[0][0]); in transpose_x8()
61 tmp2 = _mm512_loadu_si512(&ips[4][0]); in transpose_x8()
105 transpose_x16(ips, &first_1, &second_1, &third_1, &fourth_1); in trie_vec_lookup_x16x2()
247 transpose_x8(ips, &first_1, &second_1); in trie_vec_lookup_x8x2_8b()
[all …]
H A Ddir24_8_avx512.h9 rte_dir24_8_vec_lookup_bulk_1b(void *p, const uint32_t *ips,
13 rte_dir24_8_vec_lookup_bulk_2b(void *p, const uint32_t *ips,
17 rte_dir24_8_vec_lookup_bulk_4b(void *p, const uint32_t *ips,
21 rte_dir24_8_vec_lookup_bulk_8b(void *p, const uint32_t *ips,
H A Dtrie_avx512.h9 rte_trie_vec_lookup_bulk_2b(void *p, uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
13 rte_trie_vec_lookup_bulk_4b(void *p, uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
17 rte_trie_vec_lookup_bulk_8b(void *p, uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
H A Dtrie.h108 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE], \
116 tmp = ((type *)dp->tbl24)[get_tbl24_idx(&ips[i][0])]; \
119 tmp = ((type *)dp->tbl8)[ips[i][j++] + \
H A Drte_fib.c49 dummy_lookup(void *fib_p, const uint32_t *ips, uint64_t *next_hops, in dummy_lookup() argument
57 node = rte_rib_lookup(fib->rib, ips[i]); in dummy_lookup()
137 rte_fib_lookup_bulk(struct rte_fib *fib, uint32_t *ips, in rte_fib_lookup_bulk() argument
140 FIB_RETURN_IF_TRUE(((fib == NULL) || (ips == NULL) || in rte_fib_lookup_bulk()
143 fib->lookup(fib->dp, ips, next_hops, n); in rte_fib_lookup_bulk()
H A Drte_fib6.c49 dummy_lookup(void *fib_p, uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE], in dummy_lookup()
57 node = rte_rib6_lookup(fib->rib, ips[i]); in dummy_lookup()
139 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE], in rte_fib6_lookup_bulk()
142 FIB6_RETURN_IF_TRUE((fib == NULL) || (ips == NULL) || in rte_fib6_lookup_bulk()
144 fib->lookup(fib->dp, ips, next_hops, n); in rte_fib6_lookup_bulk()
H A Drte_fib.h41 typedef void (*rte_fib_lookup_fn_t)(void *fib, const uint32_t *ips,
182 rte_fib_lookup_bulk(struct rte_fib *fib, uint32_t *ips,
H A Drte_fib6.h44 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
176 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
/dpdk/examples/ipsec-secgw/
H A Dipsec.c59 struct rte_ipsec_session *ips) in create_lookaside_session() argument
93 .action_type = ips->type, in create_lookaside_session()
166 .action_type = ips->type, in create_inline_session()
283 ips->security.ctx = sec_ctx; in create_inline_session()
408 (ips->security.ol_flags & in create_inline_session()
617 switch (ips->type) { in ipsec_enqueue()
643 ips->security.ses); in ipsec_enqueue()
666 ips->crypto.ses); in ipsec_enqueue()
680 ips->security.ctx, ips->security.ses, in ipsec_enqueue()
690 ips->security.ses); in ipsec_enqueue()
[all …]
H A Dipsec_process.c265 satp = rte_ipsec_sa_type(ips->sa); in ipsec_process_inline_group()
268 k = rte_ipsec_pkt_process(ips, mb, cnt); in ipsec_process_inline_group()
284 satp = rte_ipsec_sa_type(ips->sa); in ipsec_process_cpu_group()
287 k = rte_ipsec_pkt_cpu_prepare(ips, mb, cnt); in ipsec_process_cpu_group()
288 k = rte_ipsec_pkt_process(ips, mb, k); in ipsec_process_cpu_group()
306 struct rte_ipsec_session *ips; in ipsec_process() local
325 if (sa == NULL || (ips->crypto.ses == NULL && in ipsec_process()
326 fill_ipsec_session(ips, ctx, sa) != 0)) in ipsec_process()
331 switch (ips->type) { in ipsec_process()
340 k = ipsec_process_inline_group(ips, sa, in ipsec_process()
[all …]
H A Desp.c152 struct rte_ipsec_session *ips; in esp_inbound_post() local
158 ips = ipsec_get_primary_session(sa); in esp_inbound_post()
161 (ips->type == RTE_SECURITY_ACTION_TYPE_INLINE_CRYPTO)) { in esp_inbound_post()
176 if (ips->type == RTE_SECURITY_ACTION_TYPE_INLINE_CRYPTO && in esp_inbound_post()
232 struct rte_ipsec_session *ips; in esp_outbound() local
237 ips = ipsec_get_primary_session(sa); in esp_outbound()
286 if (ips->type != RTE_SECURITY_ACTION_TYPE_INLINE_CRYPTO || in esp_outbound()
287 (ips->type == RTE_SECURITY_ACTION_TYPE_INLINE_CRYPTO && in esp_outbound()
288 !(ips->security.ol_flags & in esp_outbound()
354 if (ips->type == RTE_SECURITY_ACTION_TYPE_INLINE_CRYPTO) { in esp_outbound()
[all …]
H A Dsa.c728 ips->type = in parse_sa_tokens()
732 ips->type = in parse_sa_tokens()
736 ips->type = in parse_sa_tokens()
833 switch (ips->type) { in parse_sa_tokens()
867 ips->type); in parse_sa_tokens()
894 ips->type); in parse_sa_tokens()
930 if ((ips->type != RTE_SECURITY_ACTION_TYPE_NONE && ips->type != in parse_sa_tokens()
1011 switch (ips->type) { in print_one_sa_rule()
1264 if (ips->type == in sa_add_rules()
1382 if (ips->type == in sa_add_rules()
[all …]
H A Dipsec.h349 struct rte_ipsec_session *ips; in ipsec_get_action_type() local
350 ips = ipsec_get_primary_session(sa); in ipsec_get_action_type()
351 return ips->type; in ipsec_get_action_type()
409 struct rte_ipsec_session *ips);
413 struct rte_ipsec_session *ips);
H A Dipsec-secgw.c2824 struct rte_ipsec_session *ips; in ev_mode_sess_verify() local
2831 ips = ipsec_get_primary_session(&sa[i]); in ev_mode_sess_verify()
2832 if (ips->type != RTE_SECURITY_ACTION_TYPE_INLINE_PROTOCOL) in ev_mode_sess_verify()
2902 struct rte_ipsec_session *ips; in inline_sessions_free() local
2916 ips = ipsec_get_primary_session(sa); in inline_sessions_free()
2917 if (ips->type != RTE_SECURITY_ACTION_TYPE_INLINE_PROTOCOL && in inline_sessions_free()
2918 ips->type != RTE_SECURITY_ACTION_TYPE_INLINE_CRYPTO) in inline_sessions_free()
2926 ips->security.ses); in inline_sessions_free()
2930 ips->type, sa->spi); in inline_sessions_free()
/dpdk/lib/lpm/
H A Drte_lpm.h335 #define rte_lpm_lookup_bulk(lpm, ips, next_hops, n) \ argument
336 rte_lpm_lookup_bulk_func(lpm, ips, next_hops, n)
339 rte_lpm_lookup_bulk_func(const struct rte_lpm *lpm, const uint32_t *ips, in rte_lpm_lookup_bulk_func() argument
347 RTE_LPM_RETURN_IF_TRUE(((lpm == NULL) || (ips == NULL) || in rte_lpm_lookup_bulk_func()
351 tbl24_indexes[i] = ips[i] >> 8; in rte_lpm_lookup_bulk_func()
363 unsigned tbl8_index = (uint8_t)ips[i] + in rte_lpm_lookup_bulk_func()
H A Drte_lpm_sve.h16 __rte_lpm_lookup_vec(const struct rte_lpm *lpm, const uint32_t *ips, in __rte_lpm_lookup_vec() argument
26 v_ip = svld1(pg, &ips[i]); in __rte_lpm_lookup_vec()
70 uint32_t i, ips[4]; in rte_lpm_lookupx4() local
72 vst1q_s32((int32_t *)ips, ip); in rte_lpm_lookupx4()
76 __rte_lpm_lookup_vec(lpm, ips, hop, 4); in rte_lpm_lookupx4()
H A Drte_lpm6.h149 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], uint8_t *depths, unsigned n);
193 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE],
H A Drte_lpm6.c974 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], in rte_lpm6_lookup_bulk_func()
985 if ((lpm == NULL) || (ips == NULL) || (next_hops == NULL)) in rte_lpm6_lookup_bulk_func()
990 tbl24_index = (ips[i][0] << BYTES2_SIZE) | in rte_lpm6_lookup_bulk_func()
991 (ips[i][1] << BYTE_SIZE) | ips[i][2]; in rte_lpm6_lookup_bulk_func()
1000 status = lookup_step(lpm, tbl, &tbl_next, ips[i], in rte_lpm6_lookup_bulk_func()
1068 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], uint8_t *depths, in rte_lpm6_delete_bulk_func()
1075 if ((lpm == NULL) || (ips == NULL) || (depths == NULL)) in rte_lpm6_delete_bulk_func()
1079 ip6_copy_addr(masked_ip, ips[i]); in rte_lpm6_delete_bulk_func()
/dpdk/drivers/net/iavf/
H A Diavf_ethdev.c1767 struct iavf_ipsec_crypto_stats *ips) in iavf_dev_update_ipsec_xstats() argument
1775 ips->icount += stats->icount; in iavf_dev_update_ipsec_xstats()
1776 ips->ibytes += stats->ibytes; in iavf_dev_update_ipsec_xstats()
1777 ips->ierrors.count += stats->ierrors.count; in iavf_dev_update_ipsec_xstats()
1778 ips->ierrors.sad_miss += stats->ierrors.sad_miss; in iavf_dev_update_ipsec_xstats()
1779 ips->ierrors.not_processed += stats->ierrors.not_processed; in iavf_dev_update_ipsec_xstats()
1780 ips->ierrors.icv_check += stats->ierrors.icv_check; in iavf_dev_update_ipsec_xstats()
1781 ips->ierrors.ipsec_length += stats->ierrors.ipsec_length; in iavf_dev_update_ipsec_xstats()
1782 ips->ierrors.misc += stats->ierrors.misc; in iavf_dev_update_ipsec_xstats()
/dpdk/drivers/net/atlantic/hw_atl/
H A Dhw_atl_utils.h333 struct offload_ip_info ips; member