| /net/can/j1939/ |
| A D | bus.c | 102 write_lock_bh(&priv->lock); in j1939_ecu_unmap_all()
106 write_unlock_bh(&priv->lock); in j1939_ecu_unmap_all()
133 write_lock_bh(&priv->lock); in j1939_ecu_timer_handler()
143 write_unlock_bh(&priv->lock); in j1939_ecu_timer_handler()
200 read_lock_bh(&priv->lock); in j1939_ecu_get_by_addr()
202 read_unlock_bh(&priv->lock); in j1939_ecu_get_by_addr()
244 read_lock_bh(&priv->lock); in j1939_ecu_get_by_name()
246 read_unlock_bh(&priv->lock); in j1939_ecu_get_by_name()
259 read_lock_bh(&priv->lock); in j1939_name_to_addr()
281 write_lock_bh(&priv->lock); in j1939_local_ecu_get()
[all …]
|
| /net/ncsi/ |
| A D | ncsi-manage.c | 67 spin_lock_irqsave(&nc->lock, flags); in ncsi_report_link()
101 spin_lock_irqsave(&nc->lock, flags); in ncsi_channel_monitor()
119 spin_lock_irqsave(&nc->lock, flags); in ncsi_channel_monitor()
147 spin_lock_irqsave(&nc->lock, flags); in ncsi_channel_monitor()
161 spin_lock_irqsave(&nc->lock, flags); in ncsi_channel_monitor()
171 spin_lock_irqsave(&nc->lock, flags); in ncsi_start_channel_monitor()
184 spin_lock_irqsave(&nc->lock, flags); in ncsi_stop_channel_monitor()
223 spin_lock_init(&nc->lock); in ncsi_add_channel()
230 spin_lock_irqsave(&np->lock, flags); in ncsi_add_channel()
294 spin_lock_init(&np->lock); in ncsi_add_package()
[all …]
|
| A D | ncsi-aen.c | 67 spin_lock_irqsave(&nc->lock, flags); in ncsi_aen_handler_lsc()
82 spin_unlock_irqrestore(&nc->lock, flags); in ncsi_aen_handler_lsc()
96 spin_lock_irqsave(&ndp->lock, flags); in ncsi_aen_handler_lsc()
151 spin_lock_irqsave(&nc->lock, flags); in ncsi_aen_handler_cr()
154 spin_unlock_irqrestore(&nc->lock, flags); in ncsi_aen_handler_cr()
157 spin_unlock_irqrestore(&nc->lock, flags); in ncsi_aen_handler_cr()
160 spin_lock_irqsave(&nc->lock, flags); in ncsi_aen_handler_cr()
162 spin_unlock_irqrestore(&nc->lock, flags); in ncsi_aen_handler_cr()
164 spin_lock_irqsave(&ndp->lock, flags); in ncsi_aen_handler_cr()
186 spin_lock_irqsave(&nc->lock, flags); in ncsi_aen_handler_hncdsc()
[all …]
|
| /net/ipv4/ |
| A D | inet_timewait_sock.c | 54 spin_lock(lock); in inet_twsk_kill()
56 spin_unlock(lock); in inet_twsk_kill()
64 spin_lock(&bhead->lock); in inet_twsk_kill()
65 spin_lock(&bhead2->lock); in inet_twsk_kill()
68 spin_unlock(&bhead->lock); in inet_twsk_kill()
127 spin_lock(&bhead->lock); in inet_twsk_hashdance_schedule()
128 spin_lock(&bhead2->lock); in inet_twsk_hashdance_schedule()
140 spin_lock(lock); in inet_twsk_hashdance_schedule()
166 spin_unlock(lock); in inet_twsk_hashdance_schedule()
259 spin_lock(lock); in inet_twsk_deschedule_put()
[all …]
|
| A D | inet_hashtables.c | 190 spin_lock(&head->lock); in __inet_put_port()
558 spinlock_t *lock; in __inet_check_established() local
573 spin_lock(lock); in __inet_check_established()
602 spin_unlock(lock); in __inet_check_established()
614 spin_unlock(lock); in __inet_check_established()
675 spinlock_t *lock; in inet_ehash_insert() local
685 spin_lock(lock); in inet_ehash_insert()
698 spin_unlock(lock); in inet_ehash_insert()
817 spin_lock_bh(lock); in inet_unhash()
1173 spin_lock(lock); in __inet_hash_connect()
[all …]
|
| /net/bridge/ |
| A D | br_stp_timer.c | 35 spin_lock(&br->lock); in br_hello_timer_expired()
43 spin_unlock(&br->lock); in br_hello_timer_expired()
66 spin_lock(&br->lock); in br_message_age_timer_expired()
77 spin_unlock(&br->lock); in br_message_age_timer_expired()
88 spin_lock(&br->lock); in br_forward_delay_timer_expired()
102 spin_unlock(&br->lock); in br_forward_delay_timer_expired()
110 spin_lock(&br->lock); in br_tcn_timer_expired()
116 spin_unlock(&br->lock); in br_tcn_timer_expired()
125 spin_lock(&br->lock); in br_topology_change_timer_expired()
128 spin_unlock(&br->lock); in br_topology_change_timer_expired()
[all …]
|
| A D | br_stp_if.c | 53 spin_lock_bh(&br->lock); in br_stp_enable_bridge()
65 spin_unlock_bh(&br->lock); in br_stp_enable_bridge()
73 spin_lock_bh(&br->lock); in br_stp_disable_bridge()
82 spin_unlock_bh(&br->lock); in br_stp_disable_bridge()
158 spin_lock_bh(&br->lock); in br_stp_start()
178 spin_unlock_bh(&br->lock); in br_stp_start()
191 spin_lock_bh(&br->lock); in br_stp_stop()
193 spin_unlock_bh(&br->lock); in br_stp_stop()
287 spin_lock_bh(&br->lock); in br_stp_set_bridge_priority()
305 spin_unlock_bh(&br->lock); in br_stp_set_bridge_priority()
|
| /net/mptcp/ |
| A D | pm.c | 171 spin_lock_bh(&msk->pm.lock); in mptcp_pm_sport_in_anno_list()
465 spin_lock_bh(&pm->lock); in mptcp_pm_allow_new_subflow()
482 spin_lock_bh(&pm->lock); in mptcp_pm_allow_new_subflow()
488 spin_unlock_bh(&pm->lock); in mptcp_pm_allow_new_subflow()
516 spin_lock_bh(&pm->lock); in mptcp_pm_fully_established()
530 spin_unlock_bh(&pm->lock); in mptcp_pm_fully_established()
553 spin_lock_bh(&pm->lock); in mptcp_pm_subflow_established()
580 spin_lock_bh(&pm->lock); in mptcp_pm_subflow_check_next()
605 spin_lock_bh(&pm->lock); in mptcp_pm_add_addr_received()
638 spin_lock_bh(&pm->lock); in mptcp_pm_add_addr_echoed()
[all …]
|
| A D | pm_userspace.c | 21 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_free_local_addr_list()
23 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_free_local_addr_list()
56 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_append_new_local_addr()
89 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_append_new_local_addr()
136 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_local_id()
154 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_is_backup()
229 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_announce_doit()
266 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_remove_id_zero_address()
291 spin_lock_bh(&msk->pm.lock); in mptcp_pm_remove_addr_entry()
325 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
[all …]
|
| A D | token.c | 39 spinlock_t lock; member
123 spin_lock_bh(&bucket->lock); in mptcp_token_new_request()
125 spin_unlock_bh(&bucket->lock); in mptcp_token_new_request()
131 spin_unlock_bh(&bucket->lock); in mptcp_token_new_request()
164 spin_lock_bh(&bucket->lock); in mptcp_token_new_connect()
166 spin_unlock_bh(&bucket->lock); in mptcp_token_new_connect()
178 spin_unlock_bh(&bucket->lock); in mptcp_token_new_connect()
200 spin_lock_bh(&bucket->lock); in mptcp_token_accept()
207 spin_unlock_bh(&bucket->lock); in mptcp_token_accept()
360 spin_lock_bh(&bucket->lock); in mptcp_token_destroy_request()
[all …]
|
| A D | pm_kernel.c | 19 spinlock_t lock; member
365 spin_lock_bh(&msk->pm.lock); in mptcp_pm_create_subflow_or_signal_addr()
483 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_add_addr_received()
529 spin_lock_bh(&pernet->lock); in mptcp_pm_nl_append_new_local_addr()
757 spin_lock_bh(&msk->pm.lock); in mptcp_nl_add_subflow_or_signal_addr()
992 spin_lock_bh(&pernet->lock); in mptcp_pm_nl_del_addr_doit()
1036 spin_lock_bh(&msk->pm.lock); in mptcp_pm_flush_addrs_and_subflows()
1098 spin_lock_bh(&pernet->lock); in mptcp_pm_nl_flush_addrs_doit()
1184 spin_lock_bh(&pernet->lock); in mptcp_pm_nl_set_limits_doit()
1242 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_fullmesh()
[all …]
|
| /net/atm/ |
| A D | addr.c | 54 spin_lock_irqsave(&dev->lock, flags); in atm_reset_addr()
63 spin_unlock_irqrestore(&dev->lock, flags); in atm_reset_addr()
79 spin_lock_irqsave(&dev->lock, flags); in atm_add_addr()
86 spin_unlock_irqrestore(&dev->lock, flags); in atm_add_addr()
92 spin_unlock_irqrestore(&dev->lock, flags); in atm_add_addr()
97 spin_unlock_irqrestore(&dev->lock, flags); in atm_add_addr()
114 spin_lock_irqsave(&dev->lock, flags); in atm_del_addr()
129 spin_unlock_irqrestore(&dev->lock, flags); in atm_del_addr()
142 spin_lock_irqsave(&dev->lock, flags); in atm_get_addr()
151 spin_unlock_irqrestore(&dev->lock, flags); in atm_get_addr()
[all …]
|
| /net/phonet/ |
| A D | pn_dev.c | 25 spinlock_t lock; member
95 spin_lock(&pndevs->lock); in phonet_device_destroy()
101 spin_unlock(&pndevs->lock); in phonet_device_destroy()
142 spin_lock(&pndevs->lock); in phonet_address_add()
153 spin_unlock(&pndevs->lock); in phonet_address_add()
164 spin_lock(&pndevs->lock); in phonet_address_del()
175 spin_unlock(&pndevs->lock); in phonet_address_del()
382 spin_lock(&routes->lock); in phonet_route_add()
388 spin_unlock(&routes->lock); in phonet_route_add()
400 spin_lock(&routes->lock); in phonet_route_del()
[all …]
|
| /net/lapb/ |
| A D | lapb_iface.c | 133 spin_lock_init(&lapb->lock); in lapb_create_cb()
187 spin_lock_bh(&lapb->lock); in lapb_unregister()
194 spin_unlock_bh(&lapb->lock); in lapb_unregister()
218 spin_lock_bh(&lapb->lock); in lapb_getparms()
238 spin_unlock_bh(&lapb->lock); in lapb_getparms()
254 spin_lock_bh(&lapb->lock); in lapb_setparms()
293 spin_lock_bh(&lapb->lock); in lapb_connect_request()
356 spin_lock_bh(&lapb->lock); in lapb_disconnect_request()
375 spin_lock_bh(&lapb->lock); in lapb_data_request()
398 spin_lock_bh(&lapb->lock); in lapb_data_received()
[all …]
|
| /net/core/ |
| A D | gen_stats.c | 31 if (d->lock) in gnet_stats_copy()
32 spin_unlock_bh(d->lock); in gnet_stats_copy()
60 int xstats_type, spinlock_t *lock, in gnet_stats_start_copy_compat() argument
62 __acquires(lock) in gnet_stats_start_copy_compat()
72 if (lock) { in gnet_stats_start_copy_compat()
73 d->lock = lock; in gnet_stats_start_copy_compat()
74 spin_lock_bh(lock); in gnet_stats_start_copy_compat()
442 if (d->lock) in gnet_stats_copy_app()
443 spin_unlock_bh(d->lock); in gnet_stats_copy_app()
478 if (d->lock) in gnet_stats_finish_copy()
[all …]
|
| A D | gen_estimator.c | 133 spinlock_t *lock, in gen_new_estimator() argument
162 est->stats_lock = lock; in gen_new_estimator()
168 if (lock) in gen_new_estimator()
171 if (lock) in gen_new_estimator()
176 if (lock) in gen_new_estimator()
177 spin_lock_bh(lock); in gen_new_estimator()
190 if (lock) in gen_new_estimator()
191 spin_unlock_bh(lock); in gen_new_estimator()
236 spinlock_t *lock, in gen_replace_estimator() argument
240 lock, running, opt); in gen_replace_estimator()
|
| A D | neighbour.c | 153 write_lock(&n->lock); in neigh_update_gc_list()
174 write_unlock(&n->lock); in neigh_update_gc_list()
183 write_lock(&n->lock); in neigh_update_managed_list()
195 write_unlock(&n->lock); in neigh_update_managed_list()
241 write_lock(&n->lock); in neigh_remove_one()
248 write_unlock(&n->lock); in neigh_remove_one()
272 write_lock(&n->lock); in neigh_forced_gc()
387 write_lock(&n->lock); in neigh_flush_one()
414 write_unlock(&n->lock); in neigh_flush_one()
527 rwlock_init(&n->lock); in neigh_alloc()
[all …]
|
| /net/nfc/ |
| A D | rawsock.c | 20 .lock = __RW_LOCK_UNLOCKED(raw_sk_list.lock)
25 write_lock(&l->lock); in nfc_sock_link()
27 write_unlock(&l->lock); in nfc_sock_link()
32 write_lock(&l->lock); in nfc_sock_unlink()
34 write_unlock(&l->lock); in nfc_sock_unlink()
41 spin_lock_bh(&sk->sk_write_queue.lock); in rawsock_write_queue_purge()
44 spin_unlock_bh(&sk->sk_write_queue.lock); in rawsock_write_queue_purge()
159 spin_lock_bh(&sk->sk_write_queue.lock); in rawsock_data_exchange_complete()
230 spin_lock_bh(&sk->sk_write_queue.lock); in rawsock_sendmsg()
366 read_lock(&raw_sk_list.lock); in nfc_send_to_raw_sock()
[all …]
|
| /net/tipc/ |
| A D | monitor.c | 91 rwlock_t lock; member
362 write_lock_bh(&mon->lock); in tipc_mon_remove_peer()
428 write_lock_bh(&mon->lock); in tipc_mon_peer_up()
453 write_lock_bh(&mon->lock); in tipc_mon_peer_down()
522 write_lock_bh(&mon->lock); in tipc_mon_rcv()
591 read_lock_bh(&mon->lock); in tipc_mon_prep()
618 read_lock_bh(&mon->lock); in tipc_mon_get_state()
637 write_lock_bh(&mon->lock); in mon_timeout()
667 rwlock_init(&mon->lock); in tipc_mon_create()
807 read_lock_bh(&mon->lock); in tipc_nl_add_monitor_peer()
[all …]
|
| /net/smc/ |
| A D | smc_pnet.c | 116 mutex_lock(&pnettable->lock); in smc_pnet_remove_by_pnetid()
135 mutex_unlock(&pnettable->lock); in smc_pnet_remove_by_pnetid()
197 mutex_lock(&pnettable->lock); in smc_pnet_add_by_ndev()
211 mutex_unlock(&pnettable->lock); in smc_pnet_add_by_ndev()
229 mutex_lock(&pnettable->lock); in smc_pnet_remove_by_ndev()
242 mutex_unlock(&pnettable->lock); in smc_pnet_remove_by_ndev()
376 mutex_lock(&pnettable->lock); in smc_pnet_add_eth()
457 mutex_lock(&pnettable->lock); in smc_pnet_add_ib()
614 mutex_lock(&pnettable->lock); in _smc_pnet_dump()
884 mutex_init(&pnettable->lock); in smc_pnet_net_init()
[all …]
|
| /net/ipv6/ |
| A D | mip6.c | 108 spinlock_t lock; member
116 .lock = __SPIN_LOCK_UNLOCKED(mip6_report_rl.lock)
125 spin_lock(&x->lock); in mip6_destopt_input()
129 spin_unlock(&x->lock); in mip6_destopt_input()
165 spin_lock_bh(&x->lock); in mip6_destopt_output()
167 spin_unlock_bh(&x->lock); in mip6_destopt_output()
181 spin_lock_bh(&mip6_report_rl.lock); in mip6_report_rl_allow()
294 spin_lock(&x->lock); in mip6_rthdr_input()
298 spin_unlock(&x->lock); in mip6_rthdr_input()
328 spin_lock_bh(&x->lock); in mip6_rthdr_output()
[all …]
|
| /net/6lowpan/ |
| A D | debugfs.c | 75 spin_lock_bh(&t->lock); in lowpan_ctx_plen_set()
77 spin_unlock_bh(&t->lock); in lowpan_ctx_plen_set()
88 spin_lock_bh(&t->lock); in lowpan_ctx_plen_get()
90 spin_unlock_bh(&t->lock); in lowpan_ctx_plen_get()
103 spin_lock_bh(&t->lock); in lowpan_ctx_pfx_show()
113 spin_unlock_bh(&t->lock); in lowpan_ctx_pfx_show()
149 spin_lock_bh(&t->lock); in lowpan_ctx_pfx_write()
152 spin_unlock_bh(&t->lock); in lowpan_ctx_pfx_write()
201 spin_lock_bh(&t->lock); in lowpan_context_show()
210 spin_unlock_bh(&t->lock); in lowpan_context_show()
|
| /net/sunrpc/ |
| A D | sched.c | 445 spin_lock(&q->lock); in rpc_sleep_on_timeout()
447 spin_unlock(&q->lock); in rpc_sleep_on_timeout()
463 spin_lock(&q->lock); in rpc_sleep_on()
465 spin_unlock(&q->lock); in rpc_sleep_on()
479 spin_lock(&q->lock); in rpc_sleep_on_priority_timeout()
481 spin_unlock(&q->lock); in rpc_sleep_on_priority_timeout()
496 spin_lock(&q->lock); in rpc_sleep_on_priority()
498 spin_unlock(&q->lock); in rpc_sleep_on_priority()
564 spin_lock(&queue->lock); in rpc_wake_up_queued_task()
599 spin_lock(&queue->lock); in rpc_wake_up_queued_task_set_status()
[all …]
|
| /net/netfilter/ |
| A D | xt_TEE.c | 33 struct mutex lock; member
68 mutex_lock(&tn->lock); in tee_netdev_event()
87 mutex_unlock(&tn->lock); in tee_netdev_event()
122 mutex_lock(&tn->lock); in tee_tg_check()
124 mutex_unlock(&tn->lock); in tee_tg_check()
138 mutex_lock(&tn->lock); in tee_tg_destroy()
140 mutex_unlock(&tn->lock); in tee_tg_destroy()
178 mutex_init(&tn->lock); in tee_net_init()
|
| /net/sched/ |
| A D | sch_generic.c | 82 spin_lock(lock); in __skb_dequeue_bad_txq()
104 if (lock) in __skb_dequeue_bad_txq()
127 spin_lock(lock); in qdisc_enqueue_skb_bad_txq()
140 if (lock) in qdisc_enqueue_skb_bad_txq()
150 spin_lock(lock); in dev_requeue_skb()
172 if (lock) { in dev_requeue_skb()
251 if (lock) in dequeue_skb()
275 if (lock) in dequeue_skb()
667 .q.lock = __SPIN_LOCK_UNLOCKED(noop_qdisc.q.lock),
674 .lock = __SPIN_LOCK_UNLOCKED(noop_qdisc.gso_skb.lock),
[all …]
|