Home
last modified time | relevance | path

Searched refs:skc (Results 1 – 6 of 6) sorted by relevance

/linux-6.15/net/mptcp/
H A Dpm.c81 void mptcp_local_address(const struct sock_common *skc, in mptcp_local_address() argument
84 addr->family = skc->skc_family; in mptcp_local_address()
85 addr->port = htons(skc->skc_num); in mptcp_local_address()
87 addr->addr.s_addr = skc->skc_rcv_saddr; in mptcp_local_address()
90 addr->addr6 = skc->skc_v6_rcv_saddr; in mptcp_local_address()
97 addr->family = skc->skc_family; in mptcp_remote_address()
98 addr->port = skc->skc_dport; in mptcp_remote_address()
100 addr->addr.s_addr = skc->skc_daddr; in mptcp_remote_address()
103 addr->addr6 = skc->skc_v6_daddr; in mptcp_remote_address()
121 struct sock_common *skc; in mptcp_lookup_subflow_by_saddr() local
[all …]
H A Dpm_userspace.c130 struct mptcp_pm_addr_entry *skc) in mptcp_userspace_pm_get_local_id() argument
137 entry = mptcp_userspace_pm_lookup_addr(msk, &skc->addr); in mptcp_userspace_pm_get_local_id()
142 if (skc->addr.port == msk_sport) in mptcp_userspace_pm_get_local_id()
143 skc->addr.port = 0; in mptcp_userspace_pm_get_local_id()
145 return mptcp_userspace_pm_append_new_local_addr(msk, skc, true); in mptcp_userspace_pm_get_local_id()
149 struct mptcp_addr_info *skc) in mptcp_userspace_pm_is_backup() argument
155 entry = mptcp_userspace_pm_lookup_addr(msk, skc); in mptcp_userspace_pm_is_backup()
H A Dprotocol.h733 void mptcp_local_address(const struct sock_common *skc,
735 void mptcp_remote_address(const struct sock_common *skc,
1139 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
1141 struct mptcp_pm_addr_entry *skc);
1143 struct mptcp_pm_addr_entry *skc);
1144 bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
1145 bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
1146 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
H A Dpm_kernel.c697 struct mptcp_pm_addr_entry *skc) in mptcp_pm_nl_get_local_id() argument
706 entry = __lookup_addr(pernet, &skc->addr); in mptcp_pm_nl_get_local_id()
713 entry = kmemdup(skc, sizeof(*skc), GFP_ATOMIC); in mptcp_pm_nl_get_local_id()
725 bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc) in mptcp_pm_nl_is_backup() argument
732 entry = __lookup_addr(pernet, skc); in mptcp_pm_nl_is_backup()
/linux-6.15/tools/testing/selftests/bpf/progs/
H A Dbpf_iter_setsockopt.c8 #define bpf_tcp_sk(skc) ({ \ argument
9 struct sock_common *_skc = skc; \
H A Dtest_tcp_custom_syncookie.c508 struct bpf_sock *skc; in tcp_handle_ack() local
529 skc = bpf_skc_lookup_tcp(ctx->skb, &tuple, tuple_size, -1, 0); in tcp_handle_ack()
530 if (!skc) in tcp_handle_ack()
533 if (skc->state != TCP_LISTEN) in tcp_handle_ack()
536 sk = (struct sock *)bpf_skc_to_tcp_sock(skc); in tcp_handle_ack()
553 bpf_sk_release(skc); in tcp_handle_ack()