Searched refs:mptcp_sock (Results 1 - 22 of 22) sorted by relevance

/linux-master/net/mptcp/
H A Dprotocol.h259 struct mptcp_sock { struct
348 static inline void msk_owned_by_me(const struct mptcp_sock *msk)
364 container_of_const(_ptr, struct mptcp_sock, sk.icsk_inet.sk); \
368 #define mptcp_sk(ptr) container_of_const(ptr, struct mptcp_sock, sk.icsk_inet.sk)
391 const struct mptcp_sock *msk = mptcp_sk(sk);
398 struct mptcp_sock *msk = mptcp_sk(sk);
408 const struct mptcp_sock *msk = mptcp_sk(sk);
421 struct mptcp_sock *msk = mptcp_sk(sk);
452 struct mptcp_sock *msk;
550 struct sock *conn; /* parent mptcp_sock */
[all...]
H A Dtoken_test.c21 struct mptcp_sock *null_msk = NULL;
52 static struct mptcp_sock *build_msk(struct kunit *test)
54 struct mptcp_sock *msk;
57 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER);
75 struct mptcp_sock *msk = build_msk(test);
76 struct mptcp_sock *null_msk = NULL;
97 struct mptcp_sock *msk = build_msk(test);
116 struct mptcp_sock *msk = build_msk(test);
117 struct mptcp_sock *null_msk = NULL;
H A Dbpf.c15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk)
H A Dpm.c16 int mptcp_pm_announce_addr(struct mptcp_sock *msk,
44 int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list)
63 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list)
75 void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side)
85 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk)
124 static bool mptcp_pm_schedule_work(struct mptcp_sock *msk,
137 void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk)
164 void mptcp_pm_connection_closed(struct mptcp_sock *msk)
169 void mptcp_pm_subflow_established(struct mptcp_sock *msk)
186 void mptcp_pm_subflow_check_next(struct mptcp_sock *ms
[all...]
H A Dsched.c19 static int mptcp_sched_default_get_subflow(struct mptcp_sock *msk,
86 int mptcp_init_sched(struct mptcp_sock *msk,
104 void mptcp_release_sched(struct mptcp_sock *msk)
124 int mptcp_sched_get_send(struct mptcp_sock *msk)
153 int mptcp_sched_get_retrans(struct mptcp_sock *msk)
H A Dtoken.c67 static struct mptcp_sock *
154 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
192 struct mptcp_sock *msk)
214 struct mptcp_sock *msk;
246 struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token)
250 struct mptcp_sock *msk;
297 struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot,
300 struct mptcp_sock *ret = NULL;
375 void mptcp_token_destroy(struct mptcp_sock *msk)
379 struct mptcp_sock *po
[all...]
H A Dsockopt.c20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk)
51 static void sockopt_seq_inc(struct mptcp_sock *msk)
58 static int mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval,
70 static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val)
123 static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val)
138 static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val)
147 static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val)
172 static int mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname,
207 static int mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk,
251 static int mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *ms
[all...]
H A Dprotocol.c33 struct mptcp_sock msk;
52 static u64 mptcp_wnd_end(const struct mptcp_sock *msk)
67 static int __mptcp_socket_create(struct mptcp_sock *msk)
97 struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk)
157 static bool mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to,
175 struct mptcp_sock *msk = mptcp_sk(sk);
208 static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb)
321 struct mptcp_sock *msk = mptcp_sk(sk);
337 static bool __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk,
415 struct mptcp_sock *ms
[all...]
H A Dpm_netlink.c25 struct mptcp_sock *sock;
51 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk)
147 const struct mptcp_sock *msk)
169 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk)
193 unsigned int mptcp_pm_get_add_addr_signal_max(const struct mptcp_sock *msk)
201 unsigned int mptcp_pm_get_add_addr_accept_max(const struct mptcp_sock *msk)
209 unsigned int mptcp_pm_get_subflows_max(const struct mptcp_sock *msk)
217 unsigned int mptcp_pm_get_local_addr_max(const struct mptcp_sock *msk)
225 bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk)
239 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *ms
[all...]
H A Dpm_userspace.c10 void mptcp_free_local_addr_list(struct mptcp_sock *msk)
28 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk,
89 static int mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk,
110 mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock *msk, unsigned int id)
121 int mptcp_userspace_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk,
138 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk,
172 struct mptcp_sock *msk;
233 static int mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk,
273 struct mptcp_sock *msk;
338 struct mptcp_sock *ms
[all...]
H A Dsubflow.c60 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk)
71 struct mptcp_sock *msk = subflow_req->msk;
84 static struct mptcp_sock *subflow_token_join_request(struct request_sock *req)
87 struct mptcp_sock *msk;
118 static bool subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk)
416 static bool subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk)
424 struct mptcp_sock *msk = mptcp_sk(sk);
443 static void subflow_set_remote_key(struct mptcp_sock *msk,
468 struct mptcp_sock *msk = mptcp_sk(sk);
494 struct mptcp_sock *ms
[all...]
H A Dfastopen.c62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow,
H A Dmptcp_diag.c31 struct mptcp_sock *msk = NULL;
158 struct mptcp_sock *msk;
202 struct mptcp_sock *msk = mptcp_sk(sk);
H A Dsyncookies.c97 struct mptcp_sock *msk;
H A Doptions.c449 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
562 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
655 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
710 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
785 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
830 struct mptcp_sock *msk = mptcp_sk(subflow->conn);
925 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk,
1031 static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una)
1037 static void ack_update_msk(struct mptcp_sock *msk,
1078 bool mptcp_update_rcv_data_fin(struct mptcp_sock *ms
[all...]
/linux-master/include/net/
H A Dmptcp.h16 struct mptcp_sock;
109 int (*get_subflow)(struct mptcp_sock *msk,
116 void (*init)(struct mptcp_sock *msk);
117 void (*release)(struct mptcp_sock *msk);
151 void mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info);
318 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk);
320 static inline struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk) { return NULL; }
324 struct mptcp_sock { }; struct
/linux-master/tools/testing/selftests/bpf/progs/
H A Dmptcp_sock.c32 struct mptcp_sock *msk;
81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk,
/linux-master/tools/include/linux/
H A Dbtf_ids.h192 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
/linux-master/tools/testing/selftests/bpf/
H A Dbpf_tcp_helpers.h233 struct mptcp_sock { struct
/linux-master/include/linux/
H A Dbtf_ids.h255 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
/linux-master/tools/testing/selftests/bpf/prog_tests/
H A Dmptcp.c10 #include "mptcp_sock.skel.h"
159 struct mptcp_sock *sock_skel;
/linux-master/net/core/
H A Dfilter.c11778 BTF_TYPE_EMIT(struct mptcp_sock);

Completed in 427 milliseconds