/openbmc/linux/net/mptcp/ |
H A D | ctrl.c | 78 static void mptcp_pernet_set_defaults(struct mptcp_pernet *pernet) in mptcp_pernet_set_defaults() argument 80 pernet->mptcp_enabled = 1; in mptcp_pernet_set_defaults() 81 pernet->add_addr_timeout = TCP_RTO_MAX; in mptcp_pernet_set_defaults() 82 pernet->checksum_enabled = 0; in mptcp_pernet_set_defaults() 83 pernet->allow_join_initial_addr_port = 1; in mptcp_pernet_set_defaults() 84 pernet->stale_loss_cnt = 4; in mptcp_pernet_set_defaults() 85 pernet->pm_type = MPTCP_PM_TYPE_KERNEL; in mptcp_pernet_set_defaults() 86 strcpy(pernet->scheduler, "default"); in mptcp_pernet_set_defaults() 183 static int mptcp_pernet_new_table(struct net *net, struct mptcp_pernet *pernet) in mptcp_pernet_new_table() argument 195 table[0].data = &pernet->mptcp_enabled; in mptcp_pernet_new_table() [all …]
|
H A D | pm_netlink.c | 35 /* protects pernet updates */ 155 select_local_address(const struct pm_nl_pernet *pernet, in select_local_address() argument 165 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_local_address() 182 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk, in select_signal_address() argument 194 list_for_each_entry_rcu(entry, &pernet->local_addr_list, list) { in select_signal_address() 212 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_add_addr_signal_max() local 214 return READ_ONCE(pernet->add_addr_signal_max); in mptcp_pm_get_add_addr_signal_max() 220 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); in mptcp_pm_get_add_addr_accept_max() local 222 return READ_ONCE(pernet->add_addr_accept_max); in mptcp_pm_get_add_addr_accept_max() 228 struct pm_nl_pernet *pernet in mptcp_pm_get_subflows_max() local 236 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_get_local_addr_max() local 244 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_check_work_pending() local 512 __lookup_addr_by_id(struct pm_nl_pernet * pernet,unsigned int id) __lookup_addr_by_id() argument 524 __lookup_addr(struct pm_nl_pernet * pernet,const struct mptcp_addr_info * info) __lookup_addr() argument 543 struct pm_nl_pernet *pernet; mptcp_pm_create_subflow_or_signal_addr() local 670 struct pm_nl_pernet *pernet; fill_local_addresses_vec() local 970 mptcp_pm_nl_append_new_local_addr(struct pm_nl_pernet * pernet,struct mptcp_pm_addr_entry * entry,bool needs_id) mptcp_pm_nl_append_new_local_addr() argument 1137 struct pm_nl_pernet *pernet; mptcp_pm_nl_get_local_id() local 1173 struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); mptcp_pm_nl_is_backup() local 1420 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_add_addr() local 1636 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_del_addr() local 1776 __reset_counters(struct pm_nl_pernet * pernet) __reset_counters() argument 1786 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_flush_addrs() local 1843 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_addr() local 1895 struct pm_nl_pernet *pernet; mptcp_nl_cmd_dump_addrs() local 1951 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_set_limits() local 1977 struct pm_nl_pernet *pernet = genl_info_pm_nl(info); mptcp_nl_cmd_get_limits() local 2052 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); mptcp_pm_nl_set_flags() local 2524 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_init_net() local 2546 struct pm_nl_pernet *pernet = pm_nl_get_pernet(net); pm_nl_exit_net() local [all...] |
/openbmc/linux/net/netfilter/ |
H A D | nfnetlink_cttimeout.c | 102 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_new_timeout() local 120 list_for_each_entry(timeout, &pernet->nfct_timeout_list, head) { in cttimeout_new_timeout() 174 list_add_tail_rcu(&timeout->head, &pernet->nfct_timeout_list); in cttimeout_new_timeout() 229 struct nfct_timeout_pernet *pernet; in ctnl_timeout_dump() local 241 pernet = nfct_timeout_pernet(net); in ctnl_timeout_dump() 242 list_for_each_entry_rcu(cur, &pernet->nfct_timeout_list, head) { in ctnl_timeout_dump() 267 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_get_timeout() local 283 list_for_each_entry(cur, &pernet->nfct_timeout_list, head) { in cttimeout_get_timeout() 334 struct nfct_timeout_pernet *pernet = nfct_timeout_pernet(info->net); in cttimeout_del_timeout() local 340 list_for_each_entry_safe(cur, tmp, &pernet->nfct_timeout_list, in cttimeout_del_timeout() [all …]
|
/openbmc/linux/drivers/infiniband/core/ |
H A D | cma.c | 194 struct cma_pernet *pernet = cma_pernet(net); in cma_pernet_xa() local 198 return &pernet->tcp_ps; in cma_pernet_xa() 200 return &pernet->udp_ps; in cma_pernet_xa() 202 return &pernet->ipoib_ps; in cma_pernet_xa() 204 return &pernet->ib_ps; in cma_pernet_xa() 5399 struct cma_pernet *pernet = cma_pernet(net); in cma_init_net() local 5401 xa_init(&pernet->tcp_ps); in cma_init_net() 5402 xa_init(&pernet->udp_ps); in cma_init_net() 5403 xa_init(&pernet->ipoib_ps); in cma_init_net() 5404 xa_init(&pernet->ib_ps); in cma_init_net() [all …]
|
/openbmc/linux/include/net/ |
H A D | inet_hashtables.h | 179 bool pernet; member
|
/openbmc/linux/net/ipv4/ |
H A D | inet_hashtables.c | 1278 new_hashinfo->pernet = true; in inet_pernet_hashinfo_alloc() 1293 if (!hashinfo->pernet) in inet_pernet_hashinfo_free()
|
H A D | tcp_minisocks.c | 372 if (net->ipv4.tcp_death_row.hashinfo->pernet) { in tcp_twsk_purge()
|
H A D | sysctl_net_ipv4.c | 405 if (!net_eq(net, &init_net) && !hinfo->pernet) in proc_tcp_ehash_entries()
|
H A D | tcp.c | 4749 tcp_hashinfo.pernet = false; in tcp_init()
|
/openbmc/linux/net/dccp/ |
H A D | proto.c | 1218 dccp_hashinfo.pernet = false; in dccp_init()
|