Home
last modified time | relevance | path

Searched refs:te (Results 1 – 24 of 24) sorted by relevance

/dpdk/lib/meter/
H A Drte_meter.h428 te = m->te; in rte_meter_srtcm_color_blind_check()
439 m->te = te; in rte_meter_srtcm_color_blind_check()
445 m->te = te - pkt_len; in rte_meter_srtcm_color_blind_check()
450 m->te = te; in rte_meter_srtcm_color_blind_check()
470 te = m->te; in rte_meter_srtcm_color_aware_check()
481 m->te = te; in rte_meter_srtcm_color_aware_check()
492 m->te = te; in rte_meter_srtcm_color_aware_check()
609 m->te = te; in rte_meter_trtcm_rfc4115_color_blind_check()
620 m->te = te; in rte_meter_trtcm_rfc4115_color_blind_check()
653 m->te = te; in rte_meter_trtcm_rfc4115_color_aware_check()
[all …]
H A Drte_meter.c74 m->te = p->ebs; in rte_meter_srtcm_config()
159 m->te = p->ebs; in rte_meter_trtcm_rfc4115_config()
/dpdk/lib/hash/
H A Drte_fbk_hash.c42 struct rte_tailq_entry *te; in EAL_REGISTER_TAILQ() local
55 if (te == NULL) { in EAL_REGISTER_TAILQ()
76 struct rte_tailq_entry *te; in rte_fbk_hash_create() local
110 if (te != NULL) { in rte_fbk_hash_create()
115 te = rte_zmalloc("FBK_HASH_TAILQ_ENTRY", sizeof(*te), 0); in rte_fbk_hash_create()
116 if (te == NULL) { in rte_fbk_hash_create()
126 rte_free(te); in rte_fbk_hash_create()
158 te->data = (void *) ht; in rte_fbk_hash_create()
177 struct rte_tailq_entry *te; in rte_fbk_hash_free() local
194 if (te == NULL) { in rte_fbk_hash_free()
[all …]
H A Drte_thash.c215 struct rte_tailq_entry *te; in rte_thash_init_ctx() local
235 if (te != NULL) { in rte_thash_init_ctx()
241 te = rte_zmalloc("THASH_TAILQ_ENTRY", sizeof(*te), 0); in rte_thash_init_ctx()
242 if (te == NULL) { in rte_thash_init_ctx()
284 te->data = (void *)ctx; in rte_thash_init_ctx()
294 rte_free(te); in rte_thash_init_ctx()
304 struct rte_tailq_entry *te; in rte_thash_find_existing() local
318 if (te == NULL) { in rte_thash_find_existing()
329 struct rte_tailq_entry *te; in rte_thash_free_ctx() local
343 if (te != NULL) in rte_thash_free_ctx()
[all …]
H A Drte_cuckoo_hash.c60 struct rte_tailq_entry *te; in rte_hash_find_existing() local
73 if (te == NULL) { in rte_hash_find_existing()
272 if (te != NULL) { in rte_hash_create()
274 te = NULL; in rte_hash_create()
278 te = rte_zmalloc("HASH_TAILQ_ENTRY", sizeof(*te), 0); in rte_hash_create()
279 if (te == NULL) { in rte_hash_create()
463 te->data = (void *) h; in rte_hash_create()
473 rte_free(te); in rte_hash_create()
487 struct rte_tailq_entry *te; in rte_hash_free() local
503 if (te == NULL) { in rte_hash_free()
[all …]
/dpdk/lib/stack/
H A Drte_stack.c53 struct rte_tailq_entry *te; in rte_stack_create() local
83 te = rte_zmalloc("STACK_TAILQ_ENTRY", sizeof(*te), 0); in rte_stack_create()
84 if (te == NULL) { in rte_stack_create()
97 rte_free(te); in rte_stack_create()
111 rte_free(te); in rte_stack_create()
120 te->data = s; in rte_stack_create()
135 struct rte_tailq_entry *te; in rte_stack_free() local
145 if (te->data == s) in rte_stack_free()
149 if (te == NULL) { in rte_stack_free()
158 rte_free(te); in rte_stack_free()
[all …]
/dpdk/examples/l3fwd/
H A Dl3fwd_altivec.h20 __vector unsigned int te[FWDSTEP]; in processx4_step3() local
30 te[0] = *p[0]; in processx4_step3()
33 te[1] = *p[1]; in processx4_step3()
36 te[2] = *p[2]; in processx4_step3()
39 te[3] = *p[3]; in processx4_step3()
66 *p[0] = te[0]; in processx4_step3()
67 *p[1] = te[1]; in processx4_step3()
68 *p[2] = te[2]; in processx4_step3()
69 *p[3] = te[3]; in processx4_step3()
130 __vector unsigned int te, ve; in process_packet() local
[all …]
H A Dl3fwd_sse.h19 __m128i te[FWDSTEP]; in processx4_step3() local
29 te[0] = _mm_loadu_si128(p[0]); in processx4_step3()
32 te[1] = _mm_loadu_si128(p[1]); in processx4_step3()
35 te[2] = _mm_loadu_si128(p[2]); in processx4_step3()
38 te[3] = _mm_loadu_si128(p[3]); in processx4_step3()
41 te[0] = _mm_blend_epi16(te[0], ve[0], MASK_ETH); in processx4_step3()
42 te[1] = _mm_blend_epi16(te[1], ve[1], MASK_ETH); in processx4_step3()
43 te[2] = _mm_blend_epi16(te[2], ve[2], MASK_ETH); in processx4_step3()
44 te[3] = _mm_blend_epi16(te[3], ve[3], MASK_ETH); in processx4_step3()
109 __m128i te, ve; in process_packet() local
[all …]
H A Dl3fwd_neon.h19 uint32x4_t te[FWDSTEP]; in processx4_step3() local
29 te[0] = vld1q_u32(p[0]); in processx4_step3()
32 te[1] = vld1q_u32(p[1]); in processx4_step3()
35 te[2] = vld1q_u32(p[2]); in processx4_step3()
38 te[3] = vld1q_u32(p[3]); in processx4_step3()
41 ve[0] = vsetq_lane_u32(vgetq_lane_u32(te[0], 3), ve[0], 3); in processx4_step3()
42 ve[1] = vsetq_lane_u32(vgetq_lane_u32(te[1], 3), ve[1], 3); in processx4_step3()
43 ve[2] = vsetq_lane_u32(vgetq_lane_u32(te[2], 3), ve[2], 3); in processx4_step3()
112 uint32x4_t te, ve; in process_packet() local
116 te = vld1q_u32((uint32_t *)eth_hdr); in process_packet()
[all …]
/dpdk/lib/member/
H A Drte_member.c27 struct rte_tailq_entry *te; in EAL_REGISTER_TAILQ() local
40 if (te == NULL) { in EAL_REGISTER_TAILQ()
51 struct rte_tailq_entry *te; in rte_member_free() local
61 if (te == NULL) { in rte_member_free()
79 rte_free(te); in rte_member_free()
108 setsum = te->data; in rte_member_create()
114 if (te != NULL) { in rte_member_create()
116 te = NULL; in rte_member_create()
119 te = rte_zmalloc("MEMBER_TAILQ_ENTRY", sizeof(*te), 0); in rte_member_create()
120 if (te == NULL) { in rte_member_create()
[all …]
/dpdk/lib/mbuf/
H A Drte_mbuf_dyn.c284 te = rte_zmalloc("MBUF_DYNFIELD_TAILQ_ENTRY", sizeof(*te), 0); in __rte_mbuf_dynfield_register_offset()
285 if (te == NULL) { in __rte_mbuf_dynfield_register_offset()
292 rte_free(te); in __rte_mbuf_dynfield_register_offset()
302 rte_free(te); in __rte_mbuf_dynfield_register_offset()
307 te->data = mbuf_dynfield; in __rte_mbuf_dynfield_register_offset()
372 if (te == NULL) { in __mbuf_dynflag_lookup()
461 te = rte_zmalloc("MBUF_DYNFLAG_TAILQ_ENTRY", sizeof(*te), 0); in __rte_mbuf_dynflag_register_bitnum()
462 if (te == NULL) { in __rte_mbuf_dynflag_register_bitnum()
469 rte_free(te); in __rte_mbuf_dynflag_register_bitnum()
478 rte_free(te); in __rte_mbuf_dynflag_register_bitnum()
[all …]
/dpdk/lib/fib/
H A Drte_fib.c154 struct rte_tailq_entry *te; in rte_fib_create() local
187 if (te != NULL) { in rte_fib_create()
193 te = rte_zmalloc("FIB_TAILQ_ENTRY", sizeof(*te), 0); in rte_fib_create()
194 if (te == NULL) { in rte_fib_create()
223 te->data = (void *)fib; in rte_fib_create()
233 rte_free(te); in rte_fib_create()
245 struct rte_tailq_entry *te; in rte_fib_find_existing() local
258 if (te == NULL) { in rte_fib_find_existing()
282 struct rte_tailq_entry *te; in rte_fib_free() local
297 if (te != NULL) in rte_fib_free()
[all …]
H A Drte_fib6.c155 struct rte_tailq_entry *te; in rte_fib6_create() local
188 if (te != NULL) { in rte_fib6_create()
194 te = rte_zmalloc("FIB_TAILQ_ENTRY", sizeof(*te), 0); in rte_fib6_create()
195 if (te == NULL) { in rte_fib6_create()
224 te->data = (void *)fib; in rte_fib6_create()
234 rte_free(te); in rte_fib6_create()
246 struct rte_tailq_entry *te; in rte_fib6_find_existing() local
259 if (te == NULL) { in rte_fib6_find_existing()
283 struct rte_tailq_entry *te; in rte_fib6_free() local
298 if (te != NULL) in rte_fib6_free()
[all …]
/dpdk/lib/ring/
H A Drte_ring.c245 struct rte_tailq_entry *te; in rte_ring_create_elem() local
272 te = rte_zmalloc("RING_TAILQ_ENTRY", sizeof(*te), 0); in rte_ring_create_elem()
273 if (te == NULL) { in rte_ring_create_elem()
292 te->data = (void *) r; in rte_ring_create_elem()
299 rte_free(te); in rte_ring_create_elem()
320 struct rte_tailq_entry *te; in rte_ring_free() local
345 if (te->data == (void *) r) in rte_ring_free()
349 if (te == NULL) { in rte_ring_free()
358 rte_free(te); in rte_ring_free()
399 struct rte_tailq_entry *te; in rte_ring_lookup() local
[all …]
/dpdk/lib/reorder/
H A Drte_reorder.c105 struct rte_tailq_entry *te; in rte_reorder_create() local
147 if (te != NULL) in rte_reorder_create()
151 te = rte_zmalloc("REORDER_TAILQ_ENTRY", sizeof(*te), 0); in rte_reorder_create()
152 if (te == NULL) { in rte_reorder_create()
164 rte_free(te); in rte_reorder_create()
167 te->data = (void *)b; in rte_reorder_create()
203 struct rte_tailq_entry *te; in rte_reorder_free() local
218 if (te == NULL) { in rte_reorder_free()
230 rte_free(te); in rte_reorder_free()
237 struct rte_tailq_entry *te; in rte_reorder_find_existing() local
[all …]
/dpdk/lib/acl/
H A Drte_acl.c314 struct rte_tailq_entry *te; in rte_acl_find_existing() local
326 if (te == NULL) { in rte_acl_find_existing()
337 struct rte_tailq_entry *te; in rte_acl_free() local
351 if (te == NULL) { in rte_acl_free()
362 rte_free(te); in rte_acl_free()
371 struct rte_tailq_entry *te; in rte_acl_create() local
398 if (te == NULL) { in rte_acl_create()
400 te = rte_zmalloc("ACL_TAILQ_ENTRY", sizeof(*te), 0); in rte_acl_create()
402 if (te == NULL) { in rte_acl_create()
413 rte_free(te); in rte_acl_create()
[all …]
/dpdk/lib/rib/
H A Drte_rib.c397 struct rte_tailq_entry *te; in rte_rib_create() local
430 if (te != NULL) { in rte_rib_create()
436 te = rte_zmalloc("RIB_TAILQ_ENTRY", sizeof(*te), 0); in rte_rib_create()
437 if (te == NULL) { in rte_rib_create()
457 te->data = (void *)rib; in rte_rib_create()
465 rte_free(te); in rte_rib_create()
477 struct rte_tailq_entry *te; in rte_rib_find_existing() local
490 if (te == NULL) { in rte_rib_find_existing()
501 struct rte_tailq_entry *te; in rte_rib_free() local
517 if (te != NULL) in rte_rib_free()
[all …]
H A Drte_rib6.c469 struct rte_tailq_entry *te; in rte_rib6_create() local
502 if (te != NULL) { in rte_rib6_create()
508 te = rte_zmalloc("RIB6_TAILQ_ENTRY", sizeof(*te), 0); in rte_rib6_create()
509 if (te == NULL) { in rte_rib6_create()
530 te->data = (void *)rib; in rte_rib6_create()
538 rte_free(te); in rte_rib6_create()
550 struct rte_tailq_entry *te; in rte_rib6_find_existing() local
568 if (te == NULL) { in rte_rib6_find_existing()
579 struct rte_tailq_entry *te; in rte_rib6_free() local
597 if (te != NULL) in rte_rib6_free()
[all …]
/dpdk/lib/ipsec/
H A Dipsec_sad.c259 struct rte_tailq_entry *te; in rte_ipsec_sad_create() local
361 if (te != NULL) { in rte_ipsec_sad_create()
369 te = rte_zmalloc("IPSEC_SAD_TAILQ_ENTRY", sizeof(*te), 0); in rte_ipsec_sad_create()
370 if (te == NULL) { in rte_ipsec_sad_create()
377 te->data = (void *)sad; in rte_ipsec_sad_create()
388 struct rte_tailq_entry *te; in rte_ipsec_sad_find_existing() local
409 if (te == NULL) { in rte_ipsec_sad_find_existing()
420 struct rte_tailq_entry *te; in rte_ipsec_sad_destroy() local
430 if (te->data == (void *)sad) in rte_ipsec_sad_destroy()
433 if (te != NULL) in rte_ipsec_sad_destroy()
[all …]
/dpdk/lib/mempool/
H A Drte_mempool.c733 if (te != NULL) { in rte_mempool_free()
735 rte_free(te); in rte_mempool_free()
872 te = rte_zmalloc("MEMPOOL_TAILQ_ENTRY", sizeof(*te), 0); in rte_mempool_create_empty()
927 te->data = mp; in rte_mempool_create_empty()
940 rte_free(te); in rte_mempool_create_empty()
1416 cb = te->data; in rte_mempool_event_callback_register()
1423 te = rte_zmalloc("mempool_cb_tail_entry", sizeof(*te), 0); in rte_mempool_event_callback_register()
1435 rte_free(te); in rte_mempool_event_callback_register()
1442 te->data = cb; in rte_mempool_event_callback_register()
1464 cb = te->data; in rte_mempool_event_callback_unregister()
[all …]
/dpdk/lib/lpm/
H A Drte_lpm.c128 i_lpm = te->data; in rte_lpm_find_existing()
134 if (te == NULL) { in rte_lpm_find_existing()
178 if (te != NULL) { in rte_lpm_create()
190 te = rte_zmalloc("LPM_TAILQ_ENTRY", sizeof(*te), 0); in rte_lpm_create()
191 if (te == NULL) { in rte_lpm_create()
202 rte_free(te); in rte_lpm_create()
214 rte_free(te); in rte_lpm_create()
227 rte_free(te); in rte_lpm_create()
237 te->data = i_lpm; in rte_lpm_create()
272 if (te != NULL) in rte_lpm_free()
[all …]
H A Drte_lpm6.c245 struct rte_tailq_entry *te; in rte_lpm6_create() local
324 if (te != NULL) { in rte_lpm6_create()
330 te = rte_zmalloc("LPM6_TAILQ_ENTRY", sizeof(*te), 0); in rte_lpm6_create()
331 if (te == NULL) { in rte_lpm6_create()
343 rte_free(te); in rte_lpm6_create()
359 te->data = (void *) lpm; in rte_lpm6_create()
383 struct rte_tailq_entry *te; in rte_lpm6_find_existing() local
396 if (te == NULL) { in rte_lpm6_find_existing()
411 struct rte_tailq_entry *te; in rte_lpm6_free() local
427 if (te != NULL) in rte_lpm6_free()
[all …]
/dpdk/lib/efd/
H A Drte_efd.c502 struct rte_tailq_entry *te; in rte_efd_create() local
540 TAILQ_FOREACH(te, efd_list, next) in rte_efd_create()
548 if (te != NULL) { in rte_efd_create()
550 te = NULL; in rte_efd_create()
554 te = rte_zmalloc("EFD_TAILQ_ENTRY", sizeof(*te), 0); in rte_efd_create()
555 if (te == NULL) { in rte_efd_create()
688 te->data = (void *) table; in rte_efd_create()
711 rte_free(te); in rte_efd_create()
721 struct rte_tailq_entry *te; in rte_efd_find_existing() local
736 if (te == NULL) { in rte_efd_find_existing()
[all …]
/dpdk/lib/kni/
H A Drte_kni.c123 struct rte_tailq_entry *te; in __rte_kni_get() local
129 kni = te->data; in __rte_kni_get()
134 if (te == NULL) in __rte_kni_get()
218 struct rte_tailq_entry *te; in rte_kni_alloc() local
238 te = rte_zmalloc("KNI_TAILQ_ENTRY", sizeof(*te), 0); in rte_kni_alloc()
239 if (te == NULL) { in rte_kni_alloc()
319 te->data = kni; in rte_kni_alloc()
336 rte_free(te); in rte_kni_alloc()
417 if (te->data == kni) in rte_kni_release()
421 if (te == NULL) in rte_kni_release()
[all …]