/linux-master/net/mptcp/ |
H A D | protocol.h | 259 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 D | token_test.c | 21 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 D | bpf.c | 15 struct mptcp_sock *bpf_mptcp_sock_from_subflow(struct sock *sk)
|
H A D | pm.c | 16 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 D | sched.c | 19 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 D | token.c | 67 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 D | sockopt.c | 20 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 D | protocol.c | 33 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 D | pm_netlink.c | 25 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 D | pm_userspace.c | 10 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 D | subflow.c | 60 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 D | fastopen.c | 62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow,
|
H A D | mptcp_diag.c | 31 struct mptcp_sock *msk = NULL; 158 struct mptcp_sock *msk; 202 struct mptcp_sock *msk = mptcp_sk(sk);
|
H A D | syncookies.c | 97 struct mptcp_sock *msk;
|
H A D | options.c | 449 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 D | mptcp.h | 16 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 D | mptcp_sock.c | 32 struct mptcp_sock *msk; 81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk,
|
/linux-master/tools/include/linux/ |
H A D | btf_ids.h | 192 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
/linux-master/tools/testing/selftests/bpf/ |
H A D | bpf_tcp_helpers.h | 233 struct mptcp_sock { struct
|
/linux-master/include/linux/ |
H A D | btf_ids.h | 255 BTF_SOCK_TYPE(BTF_SOCK_TYPE_MPTCP, mptcp_sock) \
|
/linux-master/tools/testing/selftests/bpf/prog_tests/ |
H A D | mptcp.c | 10 #include "mptcp_sock.skel.h" 159 struct mptcp_sock *sock_skel;
|
/linux-master/net/core/ |
H A D | filter.c | 11778 BTF_TYPE_EMIT(struct mptcp_sock);
|