Lines Matching refs:mptcp_sock
264 struct mptcp_sock { struct
359 static inline void msk_owned_by_me(const struct mptcp_sock *msk) in msk_owned_by_me() argument
375 container_of_const(_ptr, struct mptcp_sock, sk.icsk_inet.sk); \
379 #define mptcp_sk(ptr) container_of_const(ptr, struct mptcp_sock, sk.icsk_inet.sk)
407 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_head()
414 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_send_next()
424 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_tail()
437 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rtx_head()
469 struct mptcp_sock *msk;
708 void __mptcp_subflow_fully_established(struct mptcp_sock *msk,
723 struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk);
746 int mptcp_init_sched(struct mptcp_sock *msk,
748 void mptcp_release_sched(struct mptcp_sock *msk);
751 struct sock *mptcp_subflow_get_send(struct mptcp_sock *msk);
752 struct sock *mptcp_subflow_get_retrans(struct mptcp_sock *msk);
753 int mptcp_sched_get_send(struct mptcp_sock *msk);
754 int mptcp_sched_get_retrans(struct mptcp_sock *msk);
756 static inline u64 mptcp_data_avail(const struct mptcp_sock *msk) in mptcp_data_avail()
820 void mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout);
849 void mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk);
869 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit);
870 static inline bool mptcp_data_fin_enabled(const struct mptcp_sock *msk) in mptcp_data_fin_enabled()
887 const struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_stream_memory_free()
957 void mptcp_destroy_common(struct mptcp_sock *msk, unsigned int flags);
971 struct mptcp_sock *msk);
973 struct mptcp_sock *mptcp_token_get_sock(struct net *net, u32 token);
974 struct mptcp_sock *mptcp_token_iter_next(const struct net *net, long *s_slot,
976 void mptcp_token_destroy(struct mptcp_sock *msk);
984 void mptcp_pm_data_init(struct mptcp_sock *msk);
985 void mptcp_pm_data_reset(struct mptcp_sock *msk);
994 void mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk);
995 void mptcp_pm_nl_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk);
996 void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side);
997 void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk);
998 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk);
999 void mptcp_pm_connection_closed(struct mptcp_sock *msk);
1000 void mptcp_pm_subflow_established(struct mptcp_sock *msk);
1001 bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk);
1002 void mptcp_pm_subflow_check_next(struct mptcp_sock *msk,
1006 void mptcp_pm_add_addr_echoed(struct mptcp_sock *msk,
1008 void mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk);
1009 bool mptcp_pm_nl_is_init_remote_addr(struct mptcp_sock *msk,
1011 void mptcp_pm_nl_addr_send_ack(struct mptcp_sock *msk);
1012 void mptcp_pm_rm_addr_received(struct mptcp_sock *msk,
1016 int mptcp_pm_nl_mp_prio_send_ack(struct mptcp_sock *msk,
1020 bool mptcp_pm_alloc_anno_list(struct mptcp_sock *msk,
1022 void mptcp_pm_free_anno_list(struct mptcp_sock *msk);
1023 bool mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk);
1025 mptcp_pm_del_add_timer(struct mptcp_sock *msk,
1028 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk,
1033 int mptcp_pm_announce_addr(struct mptcp_sock *msk,
1036 int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list);
1037 void mptcp_pm_remove_addrs(struct mptcp_sock *msk, struct list_head *rm_list);
1039 void mptcp_free_local_addr_list(struct mptcp_sock *msk);
1041 void mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk,
1044 void mptcp_event_addr_removed(const struct mptcp_sock *msk, u8 id);
1047 bool mptcp_userspace_pm_active(const struct mptcp_sock *msk);
1049 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow,
1056 static inline bool mptcp_pm_should_add_signal(struct mptcp_sock *msk) in mptcp_pm_should_add_signal()
1062 static inline bool mptcp_pm_should_add_signal_addr(struct mptcp_sock *msk) in mptcp_pm_should_add_signal_addr()
1067 static inline bool mptcp_pm_should_add_signal_echo(struct mptcp_sock *msk) in mptcp_pm_should_add_signal_echo()
1072 static inline bool mptcp_pm_should_rm_signal(struct mptcp_sock *msk) in mptcp_pm_should_rm_signal()
1077 static inline bool mptcp_pm_is_userspace(const struct mptcp_sock *msk) in mptcp_pm_is_userspace()
1082 static inline bool mptcp_pm_is_kernel(const struct mptcp_sock *msk) in mptcp_pm_is_kernel()
1110 bool mptcp_pm_add_addr_signal(struct mptcp_sock *msk, const struct sk_buff *skb,
1114 bool mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining,
1116 int mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc);
1117 int mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
1118 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
1119 bool mptcp_pm_is_backup(struct mptcp_sock *msk, struct sock_common *skc);
1120 bool mptcp_pm_nl_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
1121 bool mptcp_userspace_pm_is_backup(struct mptcp_sock *msk, struct mptcp_addr_info *skc);
1142 void mptcp_pm_nl_work(struct mptcp_sock *msk);
1143 unsigned int mptcp_pm_get_add_addr_signal_max(const struct mptcp_sock *msk);
1144 unsigned int mptcp_pm_get_add_addr_accept_max(const struct mptcp_sock *msk);
1145 unsigned int mptcp_pm_get_subflows_max(const struct mptcp_sock *msk);
1146 unsigned int mptcp_pm_get_local_addr_max(const struct mptcp_sock *msk);
1149 static inline void __mptcp_pm_close_subflow(struct mptcp_sock *msk) in __mptcp_pm_close_subflow()
1155 static inline void mptcp_pm_close_subflow(struct mptcp_sock *msk) in mptcp_pm_close_subflow()
1162 void mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk);
1171 static inline bool __mptcp_check_fallback(const struct mptcp_sock *msk) in __mptcp_check_fallback()
1179 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_check_fallback()
1184 static inline void __mptcp_do_fallback(struct mptcp_sock *msk) in __mptcp_do_fallback()
1193 static inline bool __mptcp_has_initial_subflow(const struct mptcp_sock *msk) in __mptcp_has_initial_subflow()
1206 struct mptcp_sock *msk; in mptcp_do_fallback()
1225 static inline void mptcp_subflow_early_fallback(struct mptcp_sock *msk, in mptcp_subflow_early_fallback()