Home
last modified time | relevance | path

Searched refs:entry (Results 1 – 25 of 111) sorted by relevance

12345

/net/atm/
A Dmpoa_caches.c48 entry = entry->next; in in_cache_get()
69 entry = entry->next; in in_cache_get_with_mask()
90 entry = entry->next; in in_cache_get_by_vcc()
201 entry->prev->next = entry->next; in in_cache_remove_entry()
278 entry = entry->next; in check_resolving_entries()
293 entry = entry->next; in check_resolving_entries()
319 entry = entry->next; in refresh_entries()
345 entry = entry->next; in eg_cache_get_by_cache_id()
366 entry = entry->next; in eg_cache_get_by_tag()
388 entry = entry->next; in eg_cache_get_by_vcc()
[all …]
A Dlec.c114 kfree(entry); in lec_arp_put()
284 entry = NULL; in lec_start_xmit()
289 if (entry && (entry->tx_wait.qlen < LEC_UNRES_QUE_LEN)) { in lec_start_xmit()
306 while (entry && (skb2 = skb_dequeue(&entry->tx_wait))) { in lec_start_xmit()
330 if (entry) in lec_start_xmit()
640 if (entry && entry->vcc != vcc) { in lec_push()
1279 entry->recv_vcc->push = entry->old_recv_push; in lec_arp_clear_vccs()
1562 entry = timer_container_of(entry, t, timer); in lec_arp_expire_arp()
1781 entry->last_used = entry->timestamp = jiffies; in lec_arp_resolve()
1996 entry->vcc ? entry->vcc->vci : 0, in lec_vcc_added()
[all …]
A Dmpc.c184 return entry; in atm_mpoa_add_qos()
190 return entry; in atm_mpoa_add_qos()
194 entry->qos = *qos; in atm_mpoa_add_qos()
197 qos_head = entry; in atm_mpoa_add_qos()
199 return entry; in atm_mpoa_add_qos()
227 kfree(entry); in atm_mpoa_delete_qos()
235 kfree(entry); in atm_mpoa_delete_qos()
560 entry->shortcut->send(entry->shortcut, skb); in send_via_shortcut()
1299 purge_egress_shortcut(entry->shortcut, entry); in mps_death()
1300 entry = entry->next; in mps_death()
[all …]
A Dclip.c90 pr_debug("%p to entry %p (neigh %p)\n", clip_vcc, entry, entry->neigh); in link_vcc()
91 clip_vcc->entry = entry; in link_vcc()
100 struct atmarp_entry *entry = clip_vcc->entry; in unlink_clip_vcc() local
103 if (!entry) { in unlink_clip_vcc()
117 if (entry->vccs) in unlink_clip_vcc()
150 if (entry->vccs || time_before(jiffies, entry->expires)) in neigh_check_cb()
222 skb->dev = clip_vcc->entry ? clip_vcc->entry->neigh->dev : clip_devs; in clip_push()
315 entry->vccs = NULL; in clip_constructor()
372 if (!entry->vccs) { in clip_start_xmit()
386 pr_debug("neigh %p, vccs %p\n", entry, entry->vccs); in clip_start_xmit()
[all …]
/net/netlabel/
A Dnetlabel_domainhash.c179 return entry; in netlbl_domhsh_search_def()
182 if (entry != NULL && entry->valid) in netlbl_domhsh_search_def()
183 return entry; in netlbl_domhsh_search_def()
187 if (entry != NULL && entry->valid) in netlbl_domhsh_search_def()
188 return entry; in netlbl_domhsh_search_def()
222 entry->domain ? entry->domain : "(default)"); in netlbl_domhsh_audit_add()
286 if (entry->family != AF_INET && entry->family != AF_INET6 && in netlbl_domhsh_validate()
293 if (entry->def.cipso != NULL || entry->def.calipso != NULL || in netlbl_domhsh_validate()
616 entry->domain ? entry->domain : "(default)"); in netlbl_domhsh_remove_entry()
707 kfree(entry); in netlbl_domhsh_remove_af4()
[all …]
A Dnetlabel_addrlist.c154 iter->addr == entry->addr && iter->mask == entry->mask) in netlbl_af4list_add()
223 entry->valid = 0; in netlbl_af4list_remove_entry()
224 list_del_rcu(&entry->list); in netlbl_af4list_remove_entry()
242 struct netlbl_af4list *entry; in netlbl_af4list_remove() local
245 if (entry == NULL) in netlbl_af4list_remove()
248 return entry; in netlbl_af4list_remove()
263 entry->valid = 0; in netlbl_af6list_remove_entry()
264 list_del_rcu(&entry->list); in netlbl_af6list_remove_entry()
283 struct netlbl_af6list *entry; in netlbl_af6list_remove() local
286 if (entry == NULL) in netlbl_af6list_remove()
[all …]
A Dnetlabel_kapi.c107 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in netlbl_cfg_unlbl_map_add()
108 if (entry == NULL) in netlbl_cfg_unlbl_map_add()
115 entry->family = family; in netlbl_cfg_unlbl_map_add()
183 kfree(entry->domain); in netlbl_cfg_unlbl_map_add()
184 kfree(entry); in netlbl_cfg_unlbl_map_add()
339 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in netlbl_cfg_cipsov4_map_add()
340 if (entry == NULL) in netlbl_cfg_cipsov4_map_add()
391 kfree(entry); in netlbl_cfg_cipsov4_map_add()
465 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in netlbl_cfg_calipso_map_add()
466 if (entry == NULL) in netlbl_cfg_calipso_map_add()
[all …]
A Dnetlabel_mgmt.c87 struct netlbl_dom_map *entry = kzalloc(sizeof(*entry), GFP_KERNEL); in netlbl_mgmt_add_common() local
89 if (!entry) in netlbl_mgmt_add_common()
99 nla_strscpy(entry->domain, in netlbl_mgmt_add_common()
108 switch (entry->def.type) { in netlbl_mgmt_add_common()
110 entry->family = in netlbl_mgmt_add_common()
122 entry->family = AF_INET; in netlbl_mgmt_add_common()
134 entry->family = AF_INET6; in netlbl_mgmt_add_common()
189 entry->family = AF_INET; in netlbl_mgmt_add_common()
262 kfree(entry->domain); in netlbl_mgmt_add_common()
264 kfree(entry); in netlbl_mgmt_add_common()
[all …]
A Dnetlabel_unlabeled.c239 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in netlbl_unlhsh_add_addr4()
240 if (entry == NULL) in netlbl_unlhsh_add_addr4()
253 kfree(entry); in netlbl_unlhsh_add_addr4()
279 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in netlbl_unlhsh_add_addr6()
280 if (entry == NULL) in netlbl_unlhsh_add_addr6()
297 kfree(entry); in netlbl_unlhsh_add_addr6()
482 entry = NULL; in netlbl_unlhsh_remove_addr4()
501 if (entry == NULL) in netlbl_unlhsh_remove_addr4()
540 entry = NULL; in netlbl_unlhsh_remove_addr6()
559 if (entry == NULL) in netlbl_unlhsh_remove_addr6()
[all …]
/net/netfilter/
A Dnf_queue.c69 dev_put(entry->physin); in nf_queue_entry_release_refs()
70 dev_put(entry->physout); in nf_queue_entry_release_refs()
77 kfree(entry); in nf_queue_entry_free()
87 entry->physin = nf_bridge_get_physindev(skb, entry->state.net); in __nf_queue_entry_init_physdevs()
90 entry->physin = NULL; in __nf_queue_entry_init_physdevs()
91 entry->physout = NULL; in __nf_queue_entry_init_physdevs()
108 dev_hold(entry->physin); in nf_queue_entry_get_refs()
193 entry = kmalloc(sizeof(*entry) + route_key_size, GFP_ATOMIC); in __nf_queue()
194 if (!entry) in __nf_queue()
198 kfree(entry); in __nf_queue()
[all …]
A Dnfnetlink_queue.c217 entry = i; in find_dequeue_entry()
222 if (entry) in find_dequeue_entry()
227 return entry; in find_dequeue_entry()
286 return ip_route_me_harder(entry->state.net, entry->state.sk, in nf_ip_reroute()
355 entry->state.okfn(entry->state.net, entry->state.sk, skb); in nf_reinject()
384 ct_verdict = ct_hook->update(entry->state.net, entry->skb); in nfqnl_reinject()
937 if (!entry) in nf_queue_entry_dup()
941 return entry; in nf_queue_entry_dup()
943 kfree(entry); in nf_queue_entry_dup()
979 entry->skb = skb; in __nfqnl_enqueue_packet_gso()
[all …]
A Dnf_flow_table_offload.c208 entry->id = FLOW_ACTION_MANGLE; in flow_offload_mangle()
209 entry->mangle.htype = htype; in flow_offload_mangle()
210 entry->mangle.offset = offset; in flow_offload_mangle()
385 struct flow_action_entry *entry; in flow_offload_ipv6_mangle() local
531 entry->id = FLOW_ACTION_CSUM; in flow_offload_ipv4_checksum()
550 struct flow_action_entry *entry; in flow_offload_redirect() local
574 entry->dev = dev; in flow_offload_redirect()
582 struct flow_action_entry *entry; in flow_offload_encap_tunnel() local
597 entry->tunnel = tun_info; in flow_offload_encap_tunnel()
607 struct flow_action_entry *entry; in flow_offload_decap_tunnel() local
[all …]
/net/mptcp/
A Dpm_kernel.c238 return entry; in __lookup_addr_by_id()
251 return entry; in __lookup_addr()
282 if (entry) { in mptcp_pm_create_subflow_or_signal_addr()
518 kfree(entry); in __mptcp_pm_release_addr_entry()
707 ret = entry ? entry->addr.id : -1; in mptcp_pm_nl_get_local_id()
714 if (!entry) in mptcp_pm_nl_get_local_id()
820 if (!entry) { in mptcp_pm_nl_add_addr_doit()
994 if (!entry) { in mptcp_pm_nl_del_addr_doit()
1119 if (entry) { in mptcp_pm_nl_get_addr()
1143 if (!entry) in mptcp_pm_nl_dump_addr()
[all …]
A Dpm_userspace.c26 sock_kfree_s(sk, entry, sizeof(*entry)); in mptcp_userspace_pm_free_local_addr_list()
38 return entry; in mptcp_userspace_pm_lookup_addr()
71 e = sock_kmemdup(sk, entry, sizeof(*entry), GFP_ATOMIC); in mptcp_userspace_pm_append_new_local_addr()
105 if (!entry) in mptcp_userspace_pm_delete_local_addr()
112 sock_kfree_s(sk, entry, sizeof(*entry)); in mptcp_userspace_pm_delete_local_addr()
124 return entry; in mptcp_userspace_pm_lookup_addr_by_id()
139 if (entry) in mptcp_userspace_pm_get_local_id()
156 backup = entry && !!(entry->flags & MPTCP_PM_ADDR_FLAG_BACKUP); in mptcp_userspace_pm_is_backup()
600 if (entry) { in mptcp_userspace_pm_set_flags()
679 if (entry) { in mptcp_userspace_pm_get_addr()
[all …]
A Dpm.c144 return entry; in mptcp_lookup_anno_list_by_saddr()
157 ret = entry; in mptcp_remove_anno_list_by_saddr()
158 kfree(entry); in mptcp_remove_anno_list_by_saddr()
273 struct mptcp_pm_add_entry *entry = timer_container_of(entry, timer, in mptcp_pm_add_timer() local
286 if (!entry->addr.id) in mptcp_pm_add_timer()
300 entry->retrans_times++; in mptcp_pm_add_timer()
326 if (entry && (!check_id || entry->addr.id == addr->id)) { in mptcp_pm_del_add_timer()
330 if (!check_id && entry) in mptcp_pm_del_add_timer()
331 list_del(&entry->list); in mptcp_pm_del_add_timer()
338 return entry; in mptcp_pm_del_add_timer()
[all …]
/net/ipv4/
A Dudp_tunnel_nic.c78 return entry->use_cnt == 0 && !entry->flags; in udp_tunnel_nic_entry_is_free()
84 return entry->use_cnt && !(entry->flags & ~UDP_TUNNEL_NIC_ENTRY_FROZEN); in udp_tunnel_nic_entry_is_present()
118 entry->flags |= flag; in udp_tunnel_nic_entry_queue()
127 ti->port = entry->port; in udp_tunnel_nic_ti_from_entry()
128 ti->type = entry->type; in udp_tunnel_nic_ti_from_entry()
177 if (entry->use_cnt) in __udp_tunnel_nic_get_port()
372 if (!dodgy && !entry->use_cnt == !(entry->use_cnt - use_cnt_adj)) in udp_tunnel_nic_entry_adj()
388 entry->flags &= ~from; in udp_tunnel_nic_entry_adj()
474 entry->port = ti->port; in udp_tunnel_nic_add_new()
476 entry->use_cnt = 1; in udp_tunnel_nic_add_new()
[all …]
A Dcipso_ipv4.c134 if (entry->lsm_data) in cipso_v4_cache_entry_free()
136 kfree(entry->key); in cipso_v4_cache_entry_free()
137 kfree(entry); in cipso_v4_cache_entry_free()
203 list_del(&entry->list); in cipso_v4_cache_invalidate()
252 entry->activity += 1; in cipso_v4_cache_check()
267 __list_del(entry->list.prev, entry->list.next); in cipso_v4_cache_check()
276 prev_entry = entry; in cipso_v4_cache_check()
311 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in cipso_v4_cache_add()
312 if (!entry) in cipso_v4_cache_add()
315 if (!entry->key) { in cipso_v4_cache_add()
[all …]
/net/sched/
A Dact_gate.c191 entry->interval = interval; in fill_gate_entry()
213 entry->index = index; in parse_gate_entry()
223 list_del(&entry->list); in release_entry_list()
224 kfree(entry); in release_entry_list()
232 struct tcfg_gate_entry *entry; in parse_gate_list() local
246 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in parse_gate_list()
247 if (!entry) { in parse_gate_list()
255 kfree(entry); in parse_gate_list()
507 struct tcfg_gate_entry *entry; in tcf_gate_dump() local
592 if (!entry->gate.entries) in tcf_gate_get_entries()
[all …]
A Dsch_ingress.c82 struct bpf_mprog_entry *entry; in ingress_init() local
92 if (!entry) in ingress_init()
94 tcx_miniq_inc(entry); in ingress_init()
123 if (entry) { in ingress_destroy()
124 tcx_miniq_dec(entry); in ingress_destroy()
127 tcx_entry_free(entry); in ingress_destroy()
247 struct bpf_mprog_entry *entry; in clsact_init() local
258 if (!entry) in clsact_init()
260 tcx_miniq_inc(entry); in clsact_init()
277 if (!entry) in clsact_init()
[all …]
A Dsch_taprio.c134 cur = entry; in taprio_calculate_gate_durations()
203 kfree(entry); in taprio_free_sched_cb()
390 entry_found = entry; in find_entry_to_transmit()
415 return entry; in is_valid_interval()
506 if (!entry) { in get_packet_txtime()
845 gate_mask = entry ? entry->gate_mask : TAPRIO_ALL_GATES_OPEN; in taprio_dequeue()
946 if (unlikely(!entry || entry->end_time == oper->base_time)) { in advance_sched()
1105 entry = kzalloc(sizeof(*entry), GFP_KERNEL); in parse_sched_list()
1106 if (!entry) { in parse_sched_list()
1113 kfree(entry); in parse_sched_list()
[all …]
/net/appletalk/
A Daarp.c484 entry = aarp_alloc(); in aarp_proxy_probe_network()
486 if (!entry) in aarp_proxy_probe_network()
496 aarp_entry_get(entry); in aarp_proxy_probe_network()
500 proxies[hash] = entry; in aarp_proxy_probe_network()
522 aarp_entry_put(entry); in aarp_proxy_probe_network()
915 for (entry = table[ct]; entry; entry = entry->next) { in iter_next()
919 return entry; in iter_next()
962 else if (entry->next) in aarp_seq_next()
963 entry = entry->next; in aarp_seq_next()
970 return entry; in aarp_seq_next()
[all …]
/net/ipv6/
A Dcalipso.c103 if (entry->lsm_data) in calipso_cache_entry_free()
105 kfree(entry->key); in calipso_cache_entry_free()
106 kfree(entry); in calipso_cache_entry_free()
169 list_del(&entry->list); in calipso_cache_invalidate()
218 entry->activity += 1; in calipso_cache_check()
233 __list_del(entry->list.prev, entry->list.next); in calipso_cache_check()
242 prev_entry = entry; in calipso_cache_check()
278 entry = kzalloc(sizeof(*entry), GFP_ATOMIC); in calipso_cache_add()
279 if (!entry) in calipso_cache_add()
282 if (!entry->key) { in calipso_cache_add()
[all …]
/net/mac80211/
A Dmesh_pathtbl.c50 kfree_rcu(entry, fast_tx.rcu_head); in __mesh_fast_tx_entry_free()
442 if (!entry) in mesh_fast_tx_get()
449 if (entry) in mesh_fast_tx_get()
456 if (entry->mppath) in mesh_fast_tx_get()
458 entry->timestamp = jiffies; in mesh_fast_tx_get()
460 return entry; in mesh_fast_tx_get()
576 if (!entry) in mesh_fast_tx_cache()
581 &entry->rhash, in mesh_fast_tx_cache()
584 kfree(entry); in mesh_fast_tx_cache()
633 if (entry->mpath == mpath) in mesh_fast_tx_flush_mpath()
[all …]
/net/bluetooth/
A D6lowpan.c201 struct lowpan_btle_dev *entry; in lookup_peer() local
219 struct lowpan_btle_dev *entry; in lookup_dev() local
226 dev = entry; in lookup_dev()
463 struct lowpan_btle_dev *entry; in send_mcast_pkt() local
472 if (entry->netdev != netdev) in send_mcast_pkt()
766 struct lowpan_btle_dev *entry; in chan_close_cb() local
995 struct lowpan_btle_dev *entry; in disconnect_all_peers() local
1216 ifdown(entry->netdev); in disconnect_devices()
1218 entry->netdev->name, entry->netdev); in disconnect_devices()
1220 kfree(entry); in disconnect_devices()
[all …]
A Dhci_codec.c15 struct codec_list *entry; in hci_codec_list_add() local
17 entry = kzalloc(sizeof(*entry) + len, GFP_KERNEL); in hci_codec_list_add()
18 if (!entry) in hci_codec_list_add()
21 entry->id = sent->id; in hci_codec_list_add()
23 entry->cid = __le16_to_cpu(sent->cid); in hci_codec_list_add()
26 entry->transport = sent->transport; in hci_codec_list_add()
27 entry->len = len; in hci_codec_list_add()
28 entry->num_caps = 0; in hci_codec_list_add()
30 entry->num_caps = rp->num_caps; in hci_codec_list_add()
31 memcpy(entry->caps, caps, len); in hci_codec_list_add()
[all …]

Completed in 85 milliseconds

12345