Searched refs:pernet (Results 1 – 8 of 8) sorted by relevance
18 /* protects pernet updates */53 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_signal_max() 55 return READ_ONCE(pernet->endp_signal_max); in mptcp_pm_get_endp_signal_max() 61 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_subflow_max() 63 return READ_ONCE(pernet->endp_subflow_max); in mptcp_pm_get_endp_subflow_max() 69 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_laminar_max() 71 return READ_ONCE(pernet->endp_laminar_max); in mptcp_pm_get_endp_laminar_max() 77 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_endp_fullmesh_max() 79 return READ_ONCE(pernet->endp_fullmesh_max); in mptcp_pm_get_endp_fullmesh_max() 85 struct pm_nl_pernet *pernet in mptcp_pm_get_limit_add_addr_accepted() 52 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_endp_signal_max() local 60 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_endp_subflow_max() local 68 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_endp_laminar_max() local 76 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_endp_fullmesh_max() local 84 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_limit_add_addr_accepted() local 92 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_limit_extra_subflows() local 120 select_local_address(const struct pm_nl_pernet * pernet,const struct mptcp_sock * msk,struct mptcp_pm_local * new_local) select_local_address() argument 149 select_signal_address(struct pm_nl_pernet * pernet,const struct mptcp_sock * msk,struct mptcp_pm_local * new_local) select_signal_address() argument 264 __lookup_addr_by_id(struct pm_nl_pernet * pernet,unsigned int id) __lookup_addr_by_id() argument 277 __lookup_addr(struct pm_nl_pernet * pernet,const struct mptcp_addr_info * info) __lookup_addr() argument 301 struct pm_nl_pernet *pernet; mptcp_mpc_endpoint_setup() local 332 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_create_subflow_or_signal_addr() local 453 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); fill_local_addresses_vec_fullmesh() local 503 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); fill_local_laminar_endp() local 565 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); fill_local_addresses_vec_c_flag() local 724 mptcp_pm_nl_append_new_local_addr(struct pm_nl_pernet * pernet,struct mptcp_pm_addr_entry * entry,bool replace) mptcp_pm_nl_append_new_local_addr() argument 911 struct pm_nl_pernet *pernet; mptcp_pm_nl_get_local_id() local 938 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_is_backup() local 986 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_pm_nl_add_addr_doit() local 1156 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_pm_nl_del_addr_doit() local 1279 __reset_counters(struct pm_nl_pernet * pernet) __reset_counters() argument 1290 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_pm_nl_flush_addrs_doit() local 1318 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_pm_nl_get_addr() local 1338 struct pm_nl_pernet *pernet; mptcp_pm_nl_dump_addr() local 1385 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_pm_nl_set_limits_doit() local 1410 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_pm_nl_get_limits_doit() local 1494 struct pm_nl_pernet *pernet; mptcp_pm_nl_set_flags() local 1547 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_check_work_pending() local 1579 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_init_net() local 1600 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_exit_net() local [all...]
182 struct cma_pernet *pernet = cma_pernet(net); in cma_pernet_xa() local186 return &pernet->tcp_ps; in cma_pernet_xa()188 return &pernet->udp_ps; in cma_pernet_xa()190 return &pernet->ipoib_ps; in cma_pernet_xa()192 return &pernet->ib_ps; in cma_pernet_xa()5459 struct cma_pernet *pernet = cma_pernet(net); in cma_init_net() local5461 xa_init(&pernet->tcp_ps); in cma_init_net()5462 xa_init(&pernet->udp_ps); in cma_init_net()5463 xa_init(&pernet->ipoib_ps); in cma_init_net()5464 xa_init(&pernet->ib_ps); in cma_init_net()[all …]
177 bool pernet; member
1371 new_hashinfo->pernet = true; in inet_pernet_hashinfo_alloc() 1385 if (!hashinfo->pernet) in inet_pernet_hashinfo_free()
418 if (net->ipv4.tcp_death_row.hashinfo->pernet) { in tcp_twsk_purge()
408 if (!net_eq(net, &init_net) && !hinfo->pernet) in proc_tcp_ehash_entries()
5355 tcp_hashinfo.pernet = false; in tcp_init()