Lines Matching full:pm
13 &((__msk)->pm.userspace_pm_local_addr_list), list)
21 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_free_local_addr_list()
22 list_splice_init(&msk->pm.userspace_pm_local_addr_list, &free_list); 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()
81 list_add_tail_rcu(&e->list, &msk->pm.userspace_pm_local_addr_list); in mptcp_userspace_pm_append_new_local_addr()
82 msk->pm.local_addr_used++; in mptcp_userspace_pm_append_new_local_addr()
89 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_append_new_local_addr()
113 msk->pm.local_addr_used--; in mptcp_userspace_pm_delete_local_addr()
136 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_local_id()
138 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_local_id()
154 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_is_backup()
157 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_is_backup()
179 "userspace PM not selected"); in mptcp_userspace_pm_get_sock()
229 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_announce_doit()
232 msk->pm.add_addr_signaled++; in mptcp_pm_nl_announce_doit()
237 spin_unlock_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()
268 spin_unlock_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()
292 msk->pm.add_addr_signaled -= anno_nr; in mptcp_pm_remove_addr_entry()
294 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_remove_addr_entry()
325 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
328 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
334 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_remove_doit()
411 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_create_doit()
412 msk->pm.extra_subflows++; in mptcp_pm_nl_subflow_create_doit()
413 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_create_doit()
422 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_create_doit()
424 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_create_doit()
543 spin_lock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_destroy_doit()
545 spin_unlock_bh(&msk->pm.lock); in mptcp_pm_nl_subflow_destroy_doit()
600 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_set_flags()
608 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_set_flags()
646 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_dump_addr()
656 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_dump_addr()
679 spin_lock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_addr()
685 spin_unlock_bh(&msk->pm.lock); in mptcp_userspace_pm_get_addr()