From patchwork Wed Mar 5 10:59:41 2025 Content-Type: text/plain; charset="utf-8" MIME-Version: 1.0 Content-Transfer-Encoding: 7bit X-Patchwork-Submitter: Geliang Tang X-Patchwork-Id: 14002431 Received: from smtp.kernel.org (aws-us-west-2-korg-mail-1.web.codeaurora.org [10.30.226.201]) (using TLSv1.2 with cipher ECDHE-RSA-AES256-GCM-SHA384 (256/256 bits)) (No client certificate requested) by smtp.subspace.kernel.org (Postfix) with ESMTPS id B70A5221F29 for ; Wed, 5 Mar 2025 11:00:04 +0000 (UTC) Authentication-Results: smtp.subspace.kernel.org; arc=none smtp.client-ip=10.30.226.201 ARC-Seal: i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1741172404; cv=none; b=fHZl1w8MW+jtmJuOtGd/VqmR257vxLhxlGOu3chli/cc5txiWFfwFC/KKgbzuVwYARf7m6auWOsm8cWOoTpDxrrtw7puqEAkM4EEJzy0xiogVdn305qQiByYWLGXCmQJbXNVrc1VGg0C8dSYvl8IrGVzqNcSfkfNZOUMSmgrJl4= ARC-Message-Signature: i=1; a=rsa-sha256; d=subspace.kernel.org; s=arc-20240116; t=1741172404; c=relaxed/simple; bh=zSuEXiVONKwuaMYetO335infqWTk+Xs8P+QSlRaChUs=; h=From:To:Cc:Subject:Date:Message-ID:MIME-Version; b=FNMm3rJ1UQKVmK9zPMtZftLWutfxSr/cKClB0tjaE+Qf+FUGG2b3JHsk0jc4bG5UWAnrQpI4sFECN1X2dN9b5/I82XRZCcE1bRvy/wCcW6hws9nAH4a+YauPdvaMspQOQ2/nIUxxOzRJtR8OMUqo6EoTsYIGXO8/Lcod2Dxz98w= ARC-Authentication-Results: i=1; smtp.subspace.kernel.org; dkim=pass (2048-bit key) header.d=kernel.org header.i=@kernel.org header.b=U4bUd/D9; arc=none smtp.client-ip=10.30.226.201 Authentication-Results: smtp.subspace.kernel.org; dkim=pass (2048-bit key) header.d=kernel.org header.i=@kernel.org header.b="U4bUd/D9" Received: by smtp.kernel.org (Postfix) with ESMTPSA id 0E4D9C4CEE2; Wed, 5 Mar 2025 11:00:02 +0000 (UTC) DKIM-Signature: v=1; a=rsa-sha256; c=relaxed/simple; d=kernel.org; s=k20201202; t=1741172404; bh=zSuEXiVONKwuaMYetO335infqWTk+Xs8P+QSlRaChUs=; h=From:To:Cc:Subject:Date:From; b=U4bUd/D9ZjWJgXaHfgK9CXMbYVtfYxZZPVgnOG1+Yh/m+n50+1gerSHTnekLFVQqE CqTZxtWrT18kvNByGNIiM2FrF8x3TGVoquBkcvpiLfI/BA3BFsJ3ddTHkRGl7oGtix ZITi3RaTB9U/JmhxGCTWX6mnW7B/MI/cUArU+4WkELPqKhmUaTBJ7m75RaehmdWrlV Le/1QwXkAWYcoajTKln2NWzsbjxwqwaUhbpvhmw8XlPqHK9dgM8O5E7H9KhFQ38Te3 wqjcDWYEyQzXviZSMFUyU+xI9Y0vkQf8PtibJxxxsz8/TT+VwrLjFbEkF83gr05UIv av0+nQCYzVoNw== From: Geliang Tang To: mptcp@lists.linux.dev Cc: Geliang Tang Subject: [PATCH mptcp-next v9 00/12] BPF path manager, part 5 Date: Wed, 5 Mar 2025 18:59:41 +0800 Message-ID: X-Mailer: git-send-email 2.43.0 Precedence: bulk X-Mailing-List: mptcp@lists.linux.dev List-Id: List-Subscribe: List-Unsubscribe: MIME-Version: 1.0 From: Geliang Tang v9: - rename mptcp_pm_nl_ prefix to mptcp_pm_kernel_. - rename mptcp_userspace_pm_ prefix to mptcp_pm_userspace_. - update commit logs. v8: - address Matt's comments in v7. v7: - addresss Matt's comments in v6 [1]. - drop "type" from struct mptcp_pm_ops as Matt suggested. - map "pm_type" to new sysctl as Matt suggested. Depends on: - mptcp: pm: code reorganisation, v2 Based-on: <20250228-mptcp-pm-reorg-code-v2-0-fa8b2542b7a5@kernel.org> [1] https://patchwork.kernel.org/project/mptcp/cover/cover.1740320007.git.tanggeliang@kylinos.cn/ v6: - add "name" in struct mptcp_pm_ops. - add some "sysctl" patches. - drop "struct mptcp_pm_param". - drop "pm_type" in mptcp_pm_data. v5: - use "struct mptcp_pm_param *param" as unified parameters for all interfaces. - register in-kernel mptcp_pm_ops too. - only implement two interfaces "get_local_id" and "get_priority" in this set. v4: - include a new patch "define BPF path manager type". - add new interfaces: created established closed listerner_created listener_closed - rename interfaces as: address_announced address_removed subflow_established subflow_closed get_priority set_priority - rename functions as: mptcp_pm_validate mptcp_pm_register mptcp_pm_unregister mptcp_pm_initialize mptcp_pm_release v3: - rename the 2nd parameter of get_local_id() from 'local' to 'skc'. - keep the 'msk_sport' check in mptcp_userspace_pm_get_local_id(). - return 'err' instead of '0' in userspace_pm_subflow_create(). - drop 'ret' variable inmptcp_pm_data_reset(). - fix typos in commit log. v2: - update get_local_id interface in patch 2. get_addr() and dump_addr() interfaces of BPF userspace pm are dropped as Matt suggested. In order to implement BPF path manager, it's necessary to unify the interfaces of the path manager. This set contains some cleanups and refactoring to unify the interfaces in kernel space. Finally, define a struct mptcp_pm_ops for a path manager. Geliang Tang (12): mptcp: pm: define struct mptcp_pm_ops mptcp: sysctl: set path manager by name mptcp: sysctl: map path_manager to pm_type mptcp: sysctl: map pm_type to path_manager mptcp: sysctl: add available_path_managers mptcp: pm: in-kernel: register mptcp_pm_kernel mptcp: pm: userspace: register mptcp_pm_userspace mptcp: pm: init and release mptcp_pm_ops mptcp: pm: add get_local_id() interface mptcp: pm: add get_priority() interface selftests: mptcp: pm_type to path_manager mapping tests selftests: mptcp: add path_manager sysctl tests Documentation/networking/mptcp-sysctl.rst | 23 +++ include/net/mptcp.h | 19 +++ net/mptcp/ctrl.c | 112 +++++++++++++- net/mptcp/pm.c | 145 ++++++++++++++---- net/mptcp/pm_kernel.c | 35 ++++- net/mptcp/pm_userspace.c | 36 ++++- net/mptcp/protocol.h | 18 ++- .../testing/selftests/net/mptcp/mptcp_join.sh | 49 +++++- 8 files changed, 393 insertions(+), 44 deletions(-)