| /f-stack/app/redis-5.0.5/src/ |
| H A D | ae.c | 223 te = zmalloc(sizeof(*te)); in aeCreateTimeEvent() 233 te->next->prev = te; in aeCreateTimeEvent() 241 while(te) { in aeDeleteTimeEvent() 246 te = te->next; in aeDeleteTimeEvent() 267 while(te) { in aeSearchNearestTimer() 272 te = te->next; in aeSearchNearestTimer() 296 te = te->next; in processTimeEvents() 311 te->prev->next = te->next; in processTimeEvents() 315 te->next->prev = te->prev; in processTimeEvents() 329 te = te->next; in processTimeEvents() [all …]
|
| /f-stack/dpdk/lib/librte_meter/ |
| H A D | rte_meter.h | 428 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 …]
|
| /f-stack/dpdk/lib/librte_hash/ |
| H A D | rte_fbk_hash.c | 48 struct rte_tailq_entry *te; in EAL_REGISTER_TAILQ() local 61 if (te == NULL) { in EAL_REGISTER_TAILQ() 82 struct rte_tailq_entry *te; in rte_fbk_hash_create() local 116 if (te != NULL) { in rte_fbk_hash_create() 121 te = rte_zmalloc("FBK_HASH_TAILQ_ENTRY", sizeof(*te), 0); in rte_fbk_hash_create() 122 if (te == NULL) { in rte_fbk_hash_create() 132 rte_free(te); in rte_fbk_hash_create() 164 te->data = (void *) ht; in rte_fbk_hash_create() 183 struct rte_tailq_entry *te; in rte_fbk_hash_free() local 200 if (te == NULL) { in rte_fbk_hash_free() [all …]
|
| /f-stack/dpdk/lib/librte_stack/ |
| H A D | rte_stack.c | 55 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 …]
|
| /f-stack/dpdk/examples/l3fwd/ |
| H A D | l3fwd_altivec.h | 20 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() 129 vector unsigned int te, ve; in process_packet() local [all …]
|
| H A D | l3fwd_sse.h | 19 __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 D | l3fwd_neon.h | 19 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 …]
|
| /f-stack/dpdk/lib/librte_member/ |
| H A D | rte_member.c | 29 struct rte_tailq_entry *te; in EAL_REGISTER_TAILQ() local 42 if (te == NULL) { in EAL_REGISTER_TAILQ() 53 struct rte_tailq_entry *te; in rte_member_free() local 63 if (te == NULL) { in rte_member_free() 81 rte_free(te); in rte_member_free() 110 setsum = te->data; in rte_member_create() 116 if (te != NULL) { in rte_member_create() 118 te = NULL; in rte_member_create() 121 te = rte_zmalloc("MEMBER_TAILQ_ENTRY", sizeof(*te), 0); in rte_member_create() 122 if (te == NULL) { in rte_member_create() [all …]
|
| /f-stack/dpdk/lib/librte_mbuf/ |
| H A D | rte_mbuf_dyn.c | 282 te = rte_zmalloc("MBUF_DYNFIELD_TAILQ_ENTRY", sizeof(*te), 0); in __rte_mbuf_dynfield_register_offset() 283 if (te == NULL) { in __rte_mbuf_dynfield_register_offset() 290 rte_free(te); in __rte_mbuf_dynfield_register_offset() 300 rte_free(te); in __rte_mbuf_dynfield_register_offset() 305 te->data = mbuf_dynfield; in __rte_mbuf_dynfield_register_offset() 370 if (te == NULL) { in __mbuf_dynflag_lookup() 459 te = rte_zmalloc("MBUF_DYNFLAG_TAILQ_ENTRY", sizeof(*te), 0); in __rte_mbuf_dynflag_register_bitnum() 460 if (te == NULL) { in __rte_mbuf_dynflag_register_bitnum() 467 rte_free(te); in __rte_mbuf_dynflag_register_bitnum() 476 rte_free(te); in __rte_mbuf_dynflag_register_bitnum() [all …]
|
| /f-stack/dpdk/lib/librte_fib/ |
| H A D | rte_fib.c | 156 struct rte_tailq_entry *te; in rte_fib_create() local 189 if (te != NULL) { in rte_fib_create() 195 te = rte_zmalloc("FIB_TAILQ_ENTRY", sizeof(*te), 0); in rte_fib_create() 196 if (te == NULL) { in rte_fib_create() 225 te->data = (void *)fib; in rte_fib_create() 235 rte_free(te); in rte_fib_create() 247 struct rte_tailq_entry *te; in rte_fib_find_existing() local 260 if (te == NULL) { in rte_fib_find_existing() 284 struct rte_tailq_entry *te; in rte_fib_free() local 299 if (te != NULL) in rte_fib_free() [all …]
|
| H A D | rte_fib6.c | 157 struct rte_tailq_entry *te; in rte_fib6_create() local 190 if (te != NULL) { in rte_fib6_create() 196 te = rte_zmalloc("FIB_TAILQ_ENTRY", sizeof(*te), 0); in rte_fib6_create() 197 if (te == NULL) { in rte_fib6_create() 226 te->data = (void *)fib; in rte_fib6_create() 236 rte_free(te); in rte_fib6_create() 248 struct rte_tailq_entry *te; in rte_fib6_find_existing() local 261 if (te == NULL) { in rte_fib6_find_existing() 285 struct rte_tailq_entry *te; in rte_fib6_free() local 300 if (te != NULL) in rte_fib6_free() [all …]
|
| /f-stack/dpdk/lib/librte_reorder/ |
| H A D | rte_reorder.c | 106 struct rte_tailq_entry *te; in rte_reorder_create() local 148 if (te != NULL) in rte_reorder_create() 152 te = rte_zmalloc("REORDER_TAILQ_ENTRY", sizeof(*te), 0); in rte_reorder_create() 153 if (te == NULL) { in rte_reorder_create() 165 rte_free(te); in rte_reorder_create() 168 te->data = (void *)b; in rte_reorder_create() 206 struct rte_tailq_entry *te; in rte_reorder_free() local 221 if (te == NULL) { in rte_reorder_free() 233 rte_free(te); in rte_reorder_free() 240 struct rte_tailq_entry *te; in rte_reorder_find_existing() local [all …]
|
| /f-stack/dpdk/lib/librte_ring/ |
| H A D | rte_ring.c | 254 struct rte_tailq_entry *te; in rte_ring_create_elem() local 281 te = rte_zmalloc("RING_TAILQ_ENTRY", sizeof(*te), 0); in rte_ring_create_elem() 282 if (te == NULL) { in rte_ring_create_elem() 301 te->data = (void *) r; in rte_ring_create_elem() 308 rte_free(te); in rte_ring_create_elem() 329 struct rte_tailq_entry *te; in rte_ring_free() local 354 if (te->data == (void *) r) in rte_ring_free() 358 if (te == NULL) { in rte_ring_free() 367 rte_free(te); in rte_ring_free() 408 struct rte_tailq_entry *te; in rte_ring_lookup() local [all …]
|
| /f-stack/dpdk/lib/librte_acl/ |
| H A D | rte_acl.c | 315 struct rte_tailq_entry *te; in rte_acl_find_existing() local 327 if (te == NULL) { in rte_acl_find_existing() 338 struct rte_tailq_entry *te; in rte_acl_free() local 352 if (te == NULL) { in rte_acl_free() 363 rte_free(te); in rte_acl_free() 372 struct rte_tailq_entry *te; in rte_acl_create() local 399 if (te == NULL) { in rte_acl_create() 401 te = rte_zmalloc("ACL_TAILQ_ENTRY", sizeof(*te), 0); in rte_acl_create() 403 if (te == NULL) { in rte_acl_create() 414 rte_free(te); in rte_acl_create() [all …]
|
| /f-stack/dpdk/lib/librte_rib/ |
| H A D | rte_rib.c | 399 struct rte_tailq_entry *te; in rte_rib_create() local 432 if (te != NULL) { in rte_rib_create() 438 te = rte_zmalloc("RIB_TAILQ_ENTRY", sizeof(*te), 0); in rte_rib_create() 439 if (te == NULL) { in rte_rib_create() 459 te->data = (void *)rib; in rte_rib_create() 467 rte_free(te); in rte_rib_create() 479 struct rte_tailq_entry *te; in rte_rib_find_existing() local 492 if (te == NULL) { in rte_rib_find_existing() 503 struct rte_tailq_entry *te; in rte_rib_free() local 519 if (te != NULL) in rte_rib_free() [all …]
|
| H A D | rte_rib6.c | 458 struct rte_tailq_entry *te; in rte_rib6_create() local 491 if (te != NULL) { in rte_rib6_create() 497 te = rte_zmalloc("RIB6_TAILQ_ENTRY", sizeof(*te), 0); in rte_rib6_create() 498 if (te == NULL) { in rte_rib6_create() 519 te->data = (void *)rib; in rte_rib6_create() 527 rte_free(te); in rte_rib6_create() 539 struct rte_tailq_entry *te; in rte_rib6_find_existing() local 557 if (te == NULL) { in rte_rib6_find_existing() 568 struct rte_tailq_entry *te; in rte_rib6_free() local 586 if (te != NULL) in rte_rib6_free() [all …]
|
| /f-stack/dpdk/lib/librte_ipsec/ |
| H A D | ipsec_sad.c | 260 struct rte_tailq_entry *te; in rte_ipsec_sad_create() local 362 if (te != NULL) { in rte_ipsec_sad_create() 370 te = rte_zmalloc("IPSEC_SAD_TAILQ_ENTRY", sizeof(*te), 0); in rte_ipsec_sad_create() 371 if (te == NULL) { in rte_ipsec_sad_create() 378 te->data = (void *)sad; in rte_ipsec_sad_create() 389 struct rte_tailq_entry *te; in rte_ipsec_sad_find_existing() local 410 if (te == NULL) { in rte_ipsec_sad_find_existing() 421 struct rte_tailq_entry *te; in rte_ipsec_sad_destroy() local 434 if (te != NULL) in rte_ipsec_sad_destroy() 443 if (te != NULL) in rte_ipsec_sad_destroy() [all …]
|
| /f-stack/freebsd/netgraph/ |
| H A D | ng_car.c | 329 hinfo->te = 0; in ng_car_rcvdata() 338 hinfo->te += len - hinfo->tc; in ng_car_rcvdata() 345 hinfo->te = 0; in ng_car_rcvdata() 351 if (hinfo->te - len >= 0) { in ng_car_rcvdata() 354 hinfo->te -= len; in ng_car_rcvdata() 498 priv->upper.te = 0; in ng_car_rcvmsg() 509 priv->lower.te = 0; in ng_car_rcvmsg() 619 h->te += delta; in ng_car_refillhook() 621 h->te = h->conf.ebs; in ng_car_refillhook() 633 h->te = h->conf.ebs; in ng_car_refillhook() [all …]
|
| /f-stack/dpdk/lib/librte_kni/ |
| H A D | rte_kni.c | 125 struct rte_tailq_entry *te; in __rte_kni_get() local 131 kni = te->data; in __rte_kni_get() 136 if (te == NULL) in __rte_kni_get() 220 struct rte_tailq_entry *te; in rte_kni_alloc() local 240 te = rte_zmalloc("KNI_TAILQ_ENTRY", sizeof(*te), 0); in rte_kni_alloc() 241 if (te == NULL) { in rte_kni_alloc() 321 te->data = kni; in rte_kni_alloc() 338 rte_free(te); in rte_kni_alloc() 419 if (te->data == kni) in rte_kni_release() 423 if (te == NULL) in rte_kni_release() [all …]
|
| /f-stack/dpdk/lib/librte_lpm/ |
| H A D | rte_lpm.c | 135 i_lpm = te->data; in rte_lpm_find_existing() 141 if (te == NULL) { in rte_lpm_find_existing() 185 if (te != NULL) { in rte_lpm_create() 197 te = rte_zmalloc("LPM_TAILQ_ENTRY", sizeof(*te), 0); in rte_lpm_create() 198 if (te == NULL) { in rte_lpm_create() 209 rte_free(te); in rte_lpm_create() 221 rte_free(te); in rte_lpm_create() 234 rte_free(te); in rte_lpm_create() 244 te->data = i_lpm; in rte_lpm_create() 279 if (te != NULL) in rte_lpm_free() [all …]
|
| H A D | rte_lpm6.c | 252 struct rte_tailq_entry *te; in rte_lpm6_create() local 329 if (te != NULL) { in rte_lpm6_create() 335 te = rte_zmalloc("LPM6_TAILQ_ENTRY", sizeof(*te), 0); in rte_lpm6_create() 336 if (te == NULL) { in rte_lpm6_create() 348 rte_free(te); in rte_lpm6_create() 364 te->data = (void *) lpm; in rte_lpm6_create() 388 struct rte_tailq_entry *te; in rte_lpm6_find_existing() local 401 if (te == NULL) { in rte_lpm6_find_existing() 416 struct rte_tailq_entry *te; in rte_lpm6_free() local 432 if (te != NULL) in rte_lpm6_free() [all …]
|
| /f-stack/dpdk/lib/librte_mempool/ |
| H A D | rte_mempool.c | 706 struct rte_tailq_entry *te; in rte_mempool_free() local 715 if (te->data == (void *)mp) in rte_mempool_free() 719 if (te != NULL) { in rte_mempool_free() 721 rte_free(te); in rte_mempool_free() 845 te = rte_zmalloc("MEMPOOL_TAILQ_ENTRY", sizeof(*te), 0); in rte_mempool_create_empty() 846 if (te == NULL) { in rte_mempool_create_empty() 900 te->data = mp; in rte_mempool_create_empty() 913 rte_free(te); in rte_mempool_create_empty() 1278 struct rte_tailq_entry *te; in rte_mempool_list_dump() local 1298 struct rte_tailq_entry *te; in rte_mempool_lookup() local [all …]
|
| /f-stack/dpdk/lib/librte_efd/ |
| H A D | rte_efd.c | 505 struct rte_tailq_entry *te; in rte_efd_create() local 543 TAILQ_FOREACH(te, efd_list, next) in rte_efd_create() 551 if (te != NULL) { in rte_efd_create() 553 te = NULL; in rte_efd_create() 557 te = rte_zmalloc("EFD_TAILQ_ENTRY", sizeof(*te), 0); in rte_efd_create() 558 if (te == NULL) { in rte_efd_create() 691 te->data = (void *) table; in rte_efd_create() 714 rte_free(te); in rte_efd_create() 724 struct rte_tailq_entry *te; in rte_efd_find_existing() local 739 if (te == NULL) { in rte_efd_find_existing() [all …]
|
| /f-stack/freebsd/contrib/dpdk_rte_lpm/ |
| H A D | rte_lpm.c | 114 struct rte_tailq_entry *te; 120 TAILQ_FOREACH(te, lpm_list, next) { 121 l = te->data; 127 if (te == NULL) { 173 lpm = te->data; in rte_lpm_create() 178 if (te != NULL) { in rte_lpm_create() 185 te = rte_zmalloc("LPM_TAILQ_ENTRY", sizeof(*te), 0); in rte_lpm_create() 186 if (te == NULL) { in rte_lpm_create() 251 struct rte_tailq_entry *te; in rte_lpm_free() 263 if (te->data == (void *) lpm) in rte_lpm_free() [all …]
|
| /f-stack/tools/libutil/ |
| H A D | login_ok.c | 134 struct ttyent *te; in login_ttyok() local 138 te = getttynam(tty); /* Need group name */ in login_ttyok() 139 grp = te ? te->ty_group : NULL; in login_ttyok()
|