Home
last modified time | relevance | path

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

12

/f-stack/dpdk/lib/librte_fib/
H A Ddir24_8.h127 ips[i + prefetch_offset], nh_sz)); \
128 tmp = ((type *)dp->tbl24)[ips[i] >> 8]; \
135 tmp = ((type *)dp->tbl24)[ips[i] >> 8]; \
161 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk()
163 tmp = get_tbl8(dp, tmp, ips[i], nh_sz); in dir24_8_lookup_bulk()
168 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk()
170 tmp = get_tbl8(dp, tmp, ips[i], nh_sz); in dir24_8_lookup_bulk()
227 tmp = get_tbl24(dp, ips[i], nh_sz); in dir24_8_lookup_bulk_uni()
229 tmp = get_tbl8(dp, tmp, ips[i], nh_sz); in dir24_8_lookup_bulk_uni()
234 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()
98 transpose_x16(ips, &first, &second, &third, &fourth); in trie_vec_lookup_x16()
192 transpose_x8(ips, &first, &second); in trie_vec_lookup_x8_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.h114 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE], \
122 tmp = ((type *)dp->tbl24)[get_tbl24_idx(&ips[i][0])]; \
125 tmp = ((type *)dp->tbl8)[ips[i][j++] + \
H A Drte_fib.c51 dummy_lookup(void *fib_p, const uint32_t *ips, uint64_t *next_hops, in dummy_lookup() argument
59 node = rte_rib_lookup(fib->rib, ips[i]); in dummy_lookup()
139 rte_fib_lookup_bulk(struct rte_fib *fib, uint32_t *ips, in rte_fib_lookup_bulk() argument
142 FIB_RETURN_IF_TRUE(((fib == NULL) || (ips == NULL) || in rte_fib_lookup_bulk()
145 fib->lookup(fib->dp, ips, next_hops, n); in rte_fib_lookup_bulk()
H A Drte_fib6.c51 dummy_lookup(void *fib_p, uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE], in dummy_lookup()
59 node = rte_rib6_lookup(fib->rib, ips[i]); in dummy_lookup()
141 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE], in rte_fib6_lookup_bulk()
144 FIB6_RETURN_IF_TRUE((fib == NULL) || (ips == NULL) || in rte_fib6_lookup_bulk()
146 fib->lookup(fib->dp, ips, next_hops, n); in rte_fib6_lookup_bulk()
H A Drte_fib.h44 typedef void (*rte_fib_lookup_fn_t)(void *fib, const uint32_t *ips,
189 rte_fib_lookup_bulk(struct rte_fib *fib, uint32_t *ips,
H A Drte_fib6.h47 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
183 uint8_t ips[][RTE_FIB6_IPV6_ADDR_SIZE],
/f-stack/freebsd/contrib/ipfilter/netinet/
H A Dip_sync.c374 ips->is_hv = htonl(ips->is_hv);
375 ips->is_die = htonl(ips->is_die);
376 ips->is_pass = htonl(ips->is_pass);
377 ips->is_flags = htonl(ips->is_flags);
382 ips->is_sec = htons(ips->is_sec);
384 ips->is_auth = htons(ips->is_auth);
391 ips->is_hv = ntohl(ips->is_hv);
392 ips->is_die = ntohl(ips->is_die);
393 ips->is_pass = ntohl(ips->is_pass);
399 ips->is_sec = ntohs(ips->is_sec);
[all …]
H A Dip_htable.c1186 u_32_t msk, ips; local
1194 ips = addr->s_addr & msk;
1195 hv = IPE_V4_HASH_FN(ips, msk, iph->iph_size);
1199 (ipe->ipe_addr.in4_addr != ips)) {
1393 i6addr_t *msk, ips; local
1401 ips.i6[0] = addr->i6[0] & msk->i6[0];
1402 ips.i6[1] = addr->i6[1] & msk->i6[1];
1403 ips.i6[2] = addr->i6[2] & msk->i6[2];
1404 ips.i6[3] = addr->i6[3] & msk->i6[3];
1405 hv = IPE_V6_HASH_FN(ips.i6, msk->i6, iph->iph_size);
[all …]
/f-stack/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()
231 ips->security.ctx = sec_ctx; in create_inline_session()
337 (ips->security.ol_flags & in create_inline_session()
546 switch (ips->type) { in ipsec_enqueue()
563 ips->security.ses); in ipsec_enqueue()
586 ips->crypto.ses); in ipsec_enqueue()
600 ips->security.ctx, ips->security.ses, in ipsec_enqueue()
610 ips->security.ses); in ipsec_enqueue()
[all …]
H A Dipsec_process.c239 satp = rte_ipsec_sa_type(ips->sa); in ipsec_process_inline_group()
242 k = rte_ipsec_pkt_process(ips, mb, cnt); in ipsec_process_inline_group()
258 satp = rte_ipsec_sa_type(ips->sa); in ipsec_process_cpu_group()
261 k = rte_ipsec_pkt_cpu_prepare(ips, mb, cnt); in ipsec_process_cpu_group()
262 k = rte_ipsec_pkt_process(ips, mb, k); in ipsec_process_cpu_group()
280 struct rte_ipsec_session *ips; in ipsec_process() local
299 if (sa == NULL || (ips->crypto.ses == NULL && in ipsec_process()
300 fill_ipsec_session(ips, ctx, sa) != 0)) in ipsec_process()
305 switch (ips->type) { in ipsec_process()
314 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.c636 ips->type = in parse_sa_tokens()
640 ips->type = in parse_sa_tokens()
644 ips->type = in parse_sa_tokens()
686 APP_CHECK(ips->type == in parse_sa_tokens()
721 switch (ips->type) { in parse_sa_tokens()
755 ips->type); in parse_sa_tokens()
791 if ((ips->type != RTE_SECURITY_ACTION_TYPE_NONE && ips->type != in parse_sa_tokens()
870 switch (ips->type) { in print_one_sa_rule()
1117 if (ips->type == in sa_add_rules()
1213 if (ips->type == in sa_add_rules()
[all …]
H A Dipsec.h341 struct rte_ipsec_session *ips; in ipsec_get_action_type() local
342 ips = ipsec_get_primary_session(sa); in ipsec_get_action_type()
343 return ips->type; in ipsec_get_action_type()
401 struct rte_ipsec_session *ips);
405 struct rte_ipsec_session *ips);
/f-stack/dpdk/lib/librte_lpm/
H A Drte_lpm.h339 #define rte_lpm_lookup_bulk(lpm, ips, next_hops, n) \ argument
340 rte_lpm_lookup_bulk_func(lpm, ips, next_hops, n)
343 rte_lpm_lookup_bulk_func(const struct rte_lpm *lpm, const uint32_t *ips, in rte_lpm_lookup_bulk_func() argument
351 RTE_LPM_RETURN_IF_TRUE(((lpm == NULL) || (ips == NULL) || in rte_lpm_lookup_bulk_func()
355 tbl24_indexes[i] = ips[i] >> 8; in rte_lpm_lookup_bulk_func()
367 unsigned tbl8_index = (uint8_t)ips[i] + in rte_lpm_lookup_bulk_func()
H A Drte_lpm6.h150 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], uint8_t *depths, unsigned n);
194 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE],
H A Drte_lpm6.c979 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], in rte_lpm6_lookup_bulk_func()
990 if ((lpm == NULL) || (ips == NULL) || (next_hops == NULL)) in rte_lpm6_lookup_bulk_func()
995 tbl24_index = (ips[i][0] << BYTES2_SIZE) | in rte_lpm6_lookup_bulk_func()
996 (ips[i][1] << BYTE_SIZE) | ips[i][2]; in rte_lpm6_lookup_bulk_func()
1005 status = lookup_step(lpm, tbl, &tbl_next, ips[i], in rte_lpm6_lookup_bulk_func()
1073 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], uint8_t *depths, in rte_lpm6_delete_bulk_func()
1080 if ((lpm == NULL) || (ips == NULL) || (depths == NULL)) in rte_lpm6_delete_bulk_func()
1084 ip6_copy_addr(masked_ip, ips[i]); in rte_lpm6_delete_bulk_func()
/f-stack/freebsd/contrib/dpdk_rte_lpm/
H A Drte_lpm.h324 #define rte_lpm_lookup_bulk(lpm, ips, next_hops, n) \ argument
325 rte_lpm_lookup_bulk_func(lpm, ips, next_hops, n)
328 rte_lpm_lookup_bulk_func(const struct rte_lpm *lpm, const uint32_t *ips, in rte_lpm_lookup_bulk_func() argument
336 RTE_LPM_RETURN_IF_TRUE(((lpm == NULL) || (ips == NULL) || in rte_lpm_lookup_bulk_func()
340 tbl24_indexes[i] = ips[i] >> 8; in rte_lpm_lookup_bulk_func()
352 unsigned tbl8_index = (uint8_t)ips[i] + in rte_lpm_lookup_bulk_func()
H A Drte_lpm6.h158 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], uint8_t *depths, unsigned n);
202 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE],
H A Drte_lpm6.c987 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], in rte_lpm6_lookup_bulk_func()
998 if ((lpm == NULL) || (ips == NULL) || (next_hops == NULL)) in rte_lpm6_lookup_bulk_func()
1003 tbl24_index = (ips[i][0] << BYTES2_SIZE) | in rte_lpm6_lookup_bulk_func()
1004 (ips[i][1] << BYTE_SIZE) | ips[i][2]; in rte_lpm6_lookup_bulk_func()
1013 status = lookup_step(lpm, tbl, &tbl_next, ips[i], in rte_lpm6_lookup_bulk_func()
1094 uint8_t ips[][RTE_LPM6_IPV6_ADDR_SIZE], uint8_t *depths,
1101 if ((lpm == NULL) || (ips == NULL) || (depths == NULL))
1105 ip6_copy_addr(masked_ip, ips[i]);
/f-stack/freebsd/netgraph/
H A Dng_cisco.c282 struct in_addr *ips; in cisco_rcvmsg() local
285 2 * sizeof(*ips), M_NOWAIT); in cisco_rcvmsg()
290 ips = (struct in_addr *) resp->data; in cisco_rcvmsg()
291 ips[0] = sc->localip; in cisco_rcvmsg()
292 ips[1] = sc->localmask; in cisco_rcvmsg()
298 struct in_addr *const ips = (struct in_addr *)msg->data; in cisco_rcvmsg() local
300 if (msg->header.arglen < 2 * sizeof(*ips)) { in cisco_rcvmsg()
304 sc->localip = ips[0]; in cisco_rcvmsg()
305 sc->localmask = ips[1]; in cisco_rcvmsg()
/f-stack/freebsd/contrib/device-tree/Bindings/mfd/
H A Daxp20x.txt116 LDO_IO0 : LDO : ips-supply : GPIO 0
117 LDO_IO1 : LDO : ips-supply : GPIO 1
118 RTC_LDO : LDO : ips-supply : always on
144 LDO_IO0 : LDO : ips-supply : GPIO 0
145 LDO_IO1 : LDO : ips-supply : GPIO 1
146 RTC_LDO : LDO : ips-supply : always on
192 LDO_IO0 : LDO : ips-supply : GPIO 0
193 LDO_IO1 : LDO : ips-supply : GPIO 1
194 RTC_LDO : LDO : ips-supply : always on
221 LDO_IO0 : LDO : ips-supply : GPIO 0
[all …]

12