289 	bool		recovery;		/* closing subflow write queue reinjected */
298 	u8		pending_state; /* A subflow asked to set this sk_state,
318 				 * ONCE annotation, the subflow outside the socket
455 /* MPTCP subflow context */
495 		is_mptfo : 1,	    /* subflow is doing TFO */
504 		u8	hmac[MPTCPOPT_HMAC_LEN]; /* MPJ subflow only */
548 mptcp_subflow_tcp_sock(const struct mptcp_subflow_context *subflow)  in mptcp_subflow_tcp_sock()  argument
550 	return subflow->tcp_sock;  in mptcp_subflow_tcp_sock()
554 mptcp_subflow_ctx_reset(struct mptcp_subflow_context *subflow)  in mptcp_subflow_ctx_reset()  argument
556 	memset(&subflow->reset, 0, sizeof(subflow->reset));  in mptcp_subflow_ctx_reset()
557 	subflow->request_mptcp = 1;  in mptcp_subflow_ctx_reset()
558 	WRITE_ONCE(subflow->local_id, -1);  in mptcp_subflow_ctx_reset()
562 mptcp_subflow_get_map_offset(const struct mptcp_subflow_context *subflow)  in mptcp_subflow_get_map_offset()  argument
564 	return tcp_sk(mptcp_subflow_tcp_sock(subflow))->copied_seq -  in mptcp_subflow_get_map_offset()
565 		      subflow->ssn_offset -  in mptcp_subflow_get_map_offset()
566 		      subflow->map_subflow_seq;  in mptcp_subflow_get_map_offset()
570 mptcp_subflow_get_mapped_dsn(const struct mptcp_subflow_context *subflow)  in mptcp_subflow_get_mapped_dsn()  argument
572 	return subflow->map_seq + mptcp_subflow_get_map_offset(subflow);  in mptcp_subflow_get_mapped_dsn()
577 static inline void mptcp_subflow_delegate(struct mptcp_subflow_context *subflow, int action)  in mptcp_subflow_delegate()  argument
583 	/* the caller held the subflow bh socket lock */  in mptcp_subflow_delegate()
590 	old = set_mask_bits(&subflow->delegated_status, 0, set_bits);  in mptcp_subflow_delegate()
592 		if (WARN_ON_ONCE(!list_empty(&subflow->delegated_node)))  in mptcp_subflow_delegate()
597 		list_add_tail(&subflow->delegated_node, &delegated->head);  in mptcp_subflow_delegate()
598 		sock_hold(mptcp_subflow_tcp_sock(subflow));  in mptcp_subflow_delegate()
626 				       struct mptcp_subflow_context *subflow,
635 		     struct mptcp_subflow_context *subflow);
666 void mptcp_subflow_set_scheduled(struct mptcp_subflow_context *subflow,
697 static inline bool __mptcp_subflow_active(struct mptcp_subflow_context *subflow)  in __mptcp_subflow_active()  argument
700 	if (subflow->request_join && !subflow->fully_established)  in __mptcp_subflow_active()
703 	return __tcp_can_send(mptcp_subflow_tcp_sock(subflow));  in __mptcp_subflow_active()
706 void mptcp_subflow_set_active(struct mptcp_subflow_context *subflow);
708 bool mptcp_subflow_active(struct mptcp_subflow_context *subflow);
805 	struct mptcp_subflow_context *subflow;  in __mptcp_sync_sndbuf()  local
812 	mptcp_for_each_subflow(mptcp_sk(sk), subflow) {  in __mptcp_sync_sndbuf()
813 		ssk_sndbuf =  READ_ONCE(mptcp_subflow_tcp_sock(subflow)->sk_sndbuf);  in __mptcp_sync_sndbuf()
815 		subflow->cached_sndbuf = ssk_sndbuf;  in __mptcp_sync_sndbuf()
824 /* The called held both the msk socket and the subflow socket locks,
829 	struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk);  in __mptcp_propagate_sndbuf()  local
831 	if (READ_ONCE(ssk->sk_sndbuf) != subflow->cached_sndbuf)  in __mptcp_propagate_sndbuf()
835 /* the caller held only the subflow socket lock, either in process or
842 	struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk);  in mptcp_propagate_sndbuf()  local
844 	if (likely(READ_ONCE(ssk->sk_sndbuf) == subflow->cached_sndbuf))  in mptcp_propagate_sndbuf()
848 	mptcp_subflow_delegate(subflow, MPTCP_DELEGATE_SNDBUF);  in mptcp_propagate_sndbuf()
898 				 const struct mptcp_subflow_context *subflow);
957 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow,
959 void mptcp_fastopen_subflow_synack_set_params(struct mptcp_subflow_context *subflow,
1026 static inline u8 subflow_get_local_id(const struct mptcp_subflow_context *subflow)  in subflow_get_local_id()  argument
1028 	int local_id = READ_ONCE(subflow->local_id);  in subflow_get_local_id()
1075 	struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk);  in mptcp_check_fallback()  local
1076 	struct mptcp_sock *msk = mptcp_sk(subflow->conn);  in mptcp_check_fallback()
1101 	struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(ssk);  in mptcp_do_fallback()  local
1102 	struct sock *sk = subflow->conn;  in mptcp_do_fallback()
1133 static inline bool is_active_ssk(struct mptcp_subflow_context *subflow)  in is_active_ssk()  argument
1135 	return (subflow->request_mptcp || subflow->request_join);  in is_active_ssk()
1140 	struct mptcp_subflow_context *subflow = mptcp_subflow_ctx(sk);  in subflow_simultaneous_connect()  local
1144 	       is_active_ssk(subflow) &&  in subflow_simultaneous_connect()
1145 	       !subflow->conn_finished;  in subflow_simultaneous_connect()