/linux-master/arch/powerpc/include/asm/ |
H A D | feature-fixups.h | 57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ 63 FTR_ENTRY_LONG msk; \ 77 #define END_FTR_SECTION_NESTED(msk, val, label) \ 79 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup) 81 #define END_FTR_SECTION(msk, val) \ 82 END_FTR_SECTION_NESTED(msk, val, 97) 84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ 85 END_FTR_SECTION_NESTED((msk), (msk), label) 87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTIO [all...] |
/linux-master/tools/testing/selftests/powerpc/primitives/asm/ |
H A D | feature-fixups.h | 57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ 63 FTR_ENTRY_LONG msk; \ 77 #define END_FTR_SECTION_NESTED(msk, val, label) \ 79 MAKE_FTR_SECTION_ENTRY(msk, val, label, __ftr_fixup) 81 #define END_FTR_SECTION(msk, val) \ 82 END_FTR_SECTION_NESTED(msk, val, 97) 84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ 85 END_FTR_SECTION_NESTED((msk), (msk), label) 87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTIO [all...] |
/linux-master/net/mptcp/ |
H A D | sched.c | 19 static int mptcp_sched_default_get_subflow(struct mptcp_sock *msk, argument 24 ssk = data->reinject ? mptcp_subflow_get_retrans(msk) : 25 mptcp_subflow_get_send(msk); 108 int mptcp_init_sched(struct mptcp_sock *msk, argument 117 msk->sched = sched; 118 if (msk->sched->init) 119 msk->sched->init(msk); 121 pr_debug("sched=%s", msk->sched->name); 126 void mptcp_release_sched(struct mptcp_sock *msk) argument 146 mptcp_sched_get_send(struct mptcp_sock *msk) argument 175 mptcp_sched_get_retrans(struct mptcp_sock *msk) argument [all...] |
H A D | pm.c | 16 int mptcp_pm_announce_addr(struct mptcp_sock *msk, argument 20 u8 add_addr = READ_ONCE(msk->pm.addr_signal); 22 pr_debug("msk=%p, local_id=%d, echo=%d", msk, addr->id, echo); 24 lockdep_assert_held(&msk->pm.lock); 28 MPTCP_INC_STATS(sock_net((struct sock *)msk), 34 msk->pm.remote = *addr; 37 msk->pm.local = *addr; 40 WRITE_ONCE(msk->pm.addr_signal, add_addr); 44 int mptcp_pm_remove_addr(struct mptcp_sock *msk, cons argument 63 mptcp_pm_remove_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) argument 75 mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side) argument 85 mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) argument 124 mptcp_pm_schedule_work(struct mptcp_sock *msk, enum mptcp_pm_status new_status) argument 137 mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk) argument 164 mptcp_pm_connection_closed(struct mptcp_sock *msk) argument 169 mptcp_pm_subflow_established(struct mptcp_sock *msk) argument 186 mptcp_pm_subflow_check_next(struct mptcp_sock *msk, const struct mptcp_subflow_context *subflow) argument 222 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 251 mptcp_pm_add_addr_echoed(struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument 266 mptcp_pm_add_addr_send_ack(struct mptcp_sock *msk) argument 274 mptcp_pm_rm_addr_received(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) argument 297 struct mptcp_sock *msk; local 310 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 331 mptcp_pm_add_addr_signal(struct mptcp_sock *msk, const struct sk_buff *skb, unsigned int opt_size, unsigned int remaining, struct mptcp_addr_info *addr, bool *echo, bool *drop_other_suboptions) argument 378 mptcp_pm_rm_addr_signal(struct mptcp_sock *msk, unsigned int remaining, struct mptcp_rm_list *rm_list) argument 408 mptcp_pm_get_local_id(struct mptcp_sock *msk, struct sock_common *skc) argument 429 mptcp_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id, u8 *flags, int *ifindex) argument 466 mptcp_pm_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk) argument 510 mptcp_pm_data_reset(struct mptcp_sock *msk) argument 549 mptcp_pm_data_init(struct mptcp_sock *msk) argument [all...] |
H A D | token_test.c | 54 struct mptcp_sock *msk; local 57 msk = kunit_kzalloc(test, sizeof(struct mptcp_sock), GFP_USER); 58 KUNIT_EXPECT_NOT_ERR_OR_NULL(test, msk); 59 refcount_set(&((struct sock *)msk)->sk_refcnt, 1); 60 sock_net_set((struct sock *)msk, &init_net); 62 sk = (struct sock *)msk; 68 return msk; 75 struct mptcp_sock *msk = build_msk(test); local 80 ctx->conn = (struct sock *)msk; 81 sk = (struct sock *)msk; 97 struct mptcp_sock *msk = build_msk(test); local 116 struct mptcp_sock *msk = build_msk(test); local [all...] |
H A D | sockopt.c | 20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) argument 22 msk_owned_by_me(msk); 24 if (likely(!__mptcp_check_fallback(msk))) 27 return msk->first; 42 * Needs sync from mptcp join logic, but ssk->seq == msk->seq 44 * Set High order bits to sk_state so ssk->seq == msk->seq test 51 static void sockopt_seq_inc(struct mptcp_sock *msk) argument 53 u32 seq = (msk->setsockopt_seq + 1) & 0x00ffffff; 55 msk->setsockopt_seq = sockopt_seq_reset((struct sock *)msk) 58 mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval, unsigned int optlen, int *val) argument 70 mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val) argument 123 mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val) argument 138 mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) argument 147 mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val) argument 172 mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 205 mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 249 mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval, unsigned int optlen) argument 290 mptcp_setsockopt_sol_socket(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 387 mptcp_setsockopt_v6(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 582 mptcp_setsockopt_sol_tcp_congestion(struct mptcp_sock *msk, sockptr_t optval, unsigned int optlen) argument 625 __mptcp_setsockopt_set_val(struct mptcp_sock *msk, int max, int (*set_val)(struct sock *, int), int *msk_val, int val) argument 650 __mptcp_setsockopt_sol_tcp_cork(struct mptcp_sock *msk, int val) argument 670 __mptcp_setsockopt_sol_tcp_nodelay(struct mptcp_sock *msk, int val) argument 689 mptcp_setsockopt_sol_ip_set(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 735 mptcp_setsockopt_v4_set_tos(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 763 mptcp_setsockopt_v4(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 779 mptcp_setsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname, sockptr_t optval, unsigned int optlen) argument 801 mptcp_setsockopt_sol_tcp(struct mptcp_sock *msk, int optname, sockptr_t optval, unsigned int optlen) argument 873 struct mptcp_sock *msk = mptcp_sk(sk); local 908 mptcp_getsockopt_first_sf_only(struct mptcp_sock *msk, int level, int optname, char __user *optval, int __user *optlen) argument 935 mptcp_diag_fill_info(struct mptcp_sock *msk, struct mptcp_info *info) argument 994 mptcp_getsockopt_info(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument 1078 mptcp_getsockopt_tcpinfo(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument 1170 mptcp_getsockopt_subflow_addrs(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument 1268 mptcp_getsockopt_full_info(struct mptcp_sock *msk, char __user *optval, int __user *optlen) argument 1342 mptcp_put_int_option(struct mptcp_sock *msk, char __user *optval, int __user *optlen, int val) argument 1371 mptcp_getsockopt_sol_tcp(struct mptcp_sock *msk, int optname, char __user *optval, int __user *optlen) argument 1414 mptcp_getsockopt_v4(struct mptcp_sock *msk, int optname, char __user *optval, int __user *optlen) argument 1433 mptcp_getsockopt_sol_mptcp(struct mptcp_sock *msk, int optname, char __user *optval, int __user *optlen) argument 1453 struct mptcp_sock *msk = mptcp_sk(sk); local 1479 sync_socket_options(struct mptcp_sock *msk, struct sock *ssk) argument 1535 mptcp_sockopt_sync_locked(struct mptcp_sock *msk, struct sock *ssk) argument [all...] |
H A D | protocol.c | 34 struct mptcp_sock msk; member in struct:mptcp6_sock 53 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) argument 55 return READ_ONCE(msk->wnd_end); 68 static int __mptcp_socket_create(struct mptcp_sock *msk) argument 71 struct sock *sk = (struct sock *)msk; 79 msk->scaling_ratio = tcp_sk(ssock->sk)->scaling_ratio; 80 WRITE_ONCE(msk->first, ssock->sk); 82 list_add(&subflow->node, &msk->conn_list); 85 subflow->subflow_id = msk->subflow_id++; 89 mptcp_sock_graft(msk 98 __mptcp_nmpc_sk(struct mptcp_sock *msk) argument 158 mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to, struct sk_buff *from) argument 176 struct mptcp_sock *msk = mptcp_sk(sk); local 209 mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb) argument 322 struct mptcp_sock *msk = mptcp_sk(sk); local 338 __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk, struct sk_buff *skb, unsigned int offset, size_t copy_len) argument 416 struct mptcp_sock *msk = mptcp_sk(sk); local 425 struct mptcp_sock *msk = mptcp_sk(sk); local 448 struct mptcp_sock *msk = mptcp_sk(sk); local 521 mptcp_send_ack(struct mptcp_sock *msk) argument 552 mptcp_cleanup_rbuf(struct mptcp_sock *msk) argument 573 struct mptcp_sock *msk = mptcp_sk(sk); local 621 __mptcp_move_skbs_from_subflow(struct mptcp_sock *msk, struct sock *ssk, unsigned int *bytes) argument 716 __mptcp_ofo_queue(struct mptcp_sock *msk) argument 794 struct mptcp_sock *msk = mptcp_sk(sk); local 804 move_skbs_to_msk(struct mptcp_sock *msk, struct sock *ssk) argument 831 struct mptcp_sock *msk = mptcp_sk(sk); local 859 mptcp_subflow_joined(struct mptcp_sock *msk, struct sock *ssk) argument 866 __mptcp_finish_join(struct mptcp_sock *msk, struct sock *ssk) argument 890 struct mptcp_sock *msk = mptcp_sk(sk); local 934 mptcp_subflow_recv_lookup(const struct mptcp_sock *msk) argument 967 mptcp_frag_can_collapse_to(const struct mptcp_sock *msk, const struct page_frag *pfrag, const struct mptcp_data_frag *df) argument 995 struct mptcp_sock *msk = mptcp_sk(sk); local 1070 struct mptcp_sock *msk = mptcp_sk(sk); local 1099 mptcp_carve_data_frag(const struct mptcp_sock *msk, struct page_frag *pfrag, int orig_offset) argument 1125 mptcp_check_allowed_size(const struct mptcp_sock *msk, struct sock *ssk, u64 data_seq, int avail_size) argument 1210 mptcp_update_infinite_map(struct mptcp_sock *msk, struct sock *ssk, struct mptcp_ext *mpext) argument 1234 struct mptcp_sock *msk = mptcp_sk(sk); local 1407 mptcp_subflow_get_send(struct mptcp_sock *msk) argument 1487 mptcp_update_post_push(struct mptcp_sock *msk, struct mptcp_data_frag *dfrag, u32 sent) argument 1526 struct mptcp_sock *msk = mptcp_sk(sk); local 1570 struct mptcp_sock *msk = mptcp_sk(sk); local 1634 struct mptcp_sock *msk = mptcp_sk(sk); local 1705 struct mptcp_sock *msk = mptcp_sk(sk); local 1776 const struct mptcp_sock *msk = mptcp_sk(sk); local 1795 struct mptcp_sock *msk = mptcp_sk(sk); local 1922 __mptcp_recvmsg_mskq(struct mptcp_sock *msk, struct msghdr *msg, size_t len, int flags, struct scm_timestamping_internal *tss, int *cmsg_flags) argument 1982 mptcp_rcv_space_adjust(struct mptcp_sock *msk, int copied) argument 2079 struct mptcp_sock *msk = mptcp_sk(sk); local 2091 struct mptcp_sock *msk = mptcp_sk(sk); local 2096 __mptcp_move_skbs(struct mptcp_sock *msk) argument 2141 const struct mptcp_sock *msk = mptcp_sk(sk); local 2163 struct mptcp_sock *msk = mptcp_sk(sk); local 2280 struct mptcp_sock *msk = mptcp_sk(sk); local 2308 mptcp_subflow_get_retrans(struct mptcp_sock *msk) argument 2347 struct mptcp_sock *msk = mptcp_sk(sk); local 2417 struct mptcp_sock *msk = mptcp_sk(sk); local 2528 struct mptcp_sock *msk = mptcp_sk(sk); local 2557 mptcp_check_fastclose(struct mptcp_sock *msk) argument 2608 struct mptcp_sock *msk = mptcp_sk(sk); local 2688 mptcp_reset_tout_timer(struct mptcp_sock *msk, unsigned long fail_tout) argument 2707 mptcp_mp_fail_no_response(struct mptcp_sock *msk) argument 2726 struct mptcp_sock *msk = mptcp_sk(sk); local 2736 struct mptcp_sock *msk = container_of(work, struct mptcp_sock, work); local 2781 struct mptcp_sock *msk = mptcp_sk(sk); local 2859 struct mptcp_sock *msk = mptcp_sk(sk); local 2869 struct mptcp_sock *msk = mptcp_sk(sk); local 2963 struct mptcp_sock *msk = mptcp_sk(sk); local 2987 struct mptcp_sock *msk = mptcp_sk(sk); local 3002 struct mptcp_sock *msk = mptcp_sk(sk); local 3058 struct mptcp_sock *msk = mptcp_sk(sk); local 3140 mptcp_copy_inaddrs(struct sock *msk, const struct sock *ssk) argument 3165 struct mptcp_sock *msk = mptcp_sk(sk); local 3270 struct mptcp_sock *msk; local 3342 mptcp_rcv_space_init(struct mptcp_sock *msk, const struct sock *ssk) argument 3359 mptcp_destroy_common(struct mptcp_sock *msk, unsigned int flags) argument 3389 struct mptcp_sock *msk = mptcp_sk(sk); local 3424 struct mptcp_sock *msk = mptcp_sk(sk); variable in typeref:struct:mptcp_sock 3542 struct mptcp_sock *msk = mptcp_sk(sk); local 3554 struct mptcp_sock *msk; local 3586 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 3648 mptcp_ioctl_outq(const struct mptcp_sock *msk, u64 v) argument 3679 struct mptcp_sock *msk = mptcp_sk(sk); local 3709 mptcp_subflow_early_fallback(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow) argument 3719 struct mptcp_sock *msk = mptcp_sk(sk); local 3824 struct mptcp_sock *msk = mptcp_sk(sock->sk); local 3851 struct mptcp_sock *msk = mptcp_sk(sock->sk); local 3892 struct mptcp_sock *msk = mptcp_sk(sock->sk); local 3974 mptcp_check_writeable(struct mptcp_sock *msk) argument 3993 struct mptcp_sock *msk; local [all...] |
H A D | pm_netlink.c | 52 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) argument 54 return pm_nl_get_pernet(sock_net((struct sock *)msk)); 148 const struct mptcp_sock *msk) 152 msk_owned_by_me(msk); 159 if (!test_bit(entry->addr.id, msk->pm.id_avail_bitmap)) 170 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk) argument 177 * Note: removal from the local address list during the msk life-cycle 181 if (!test_bit(entry->addr.id, msk->pm.id_avail_bitmap)) 194 unsigned int mptcp_pm_get_add_addr_signal_max(const struct mptcp_sock *msk) argument 196 const struct pm_nl_pernet *pernet = pm_nl_get_pernet_from_msk(msk); 147 select_local_address(const struct pm_nl_pernet *pernet, const struct mptcp_sock *msk) argument 202 mptcp_pm_get_add_addr_accept_max(const struct mptcp_sock *msk) argument 210 mptcp_pm_get_subflows_max(const struct mptcp_sock *msk) argument 218 mptcp_pm_get_local_addr_max(const struct mptcp_sock *msk) argument 226 mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk) argument 240 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument 255 mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk) argument 279 struct mptcp_sock *msk = entry->sock; local 321 mptcp_pm_del_add_timer(struct mptcp_sock *msk, const struct mptcp_addr_info *addr, bool check_id) argument 339 mptcp_pm_alloc_anno_list(struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument 376 mptcp_pm_free_anno_list(struct mptcp_sock *msk) argument 397 fill_remote_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *local, bool fullmesh, struct mptcp_addr_info *addrs) argument 462 __mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, bool prio, bool backup) argument 482 mptcp_pm_send_ack(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, bool prio, bool backup) argument 514 mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk) argument 608 mptcp_pm_nl_fully_established(struct mptcp_sock *msk) argument 613 mptcp_pm_nl_subflow_established(struct mptcp_sock *msk) argument 621 fill_local_addresses_vec(struct mptcp_sock *msk, struct mptcp_addr_info *remote, struct mptcp_addr_info *addrs) argument 673 mptcp_pm_nl_add_addr_received(struct mptcp_sock *msk) argument 718 mptcp_pm_nl_addr_send_ack(struct mptcp_sock *msk) argument 734 mptcp_pm_nl_mp_prio_send_ack(struct mptcp_sock *msk, struct mptcp_addr_info *addr, struct mptcp_addr_info *rem, u8 bkup) argument 764 mptcp_local_id_match(const struct mptcp_sock *msk, u8 local_id, u8 id) argument 769 mptcp_pm_nl_rm_addr_or_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list, enum linux_mptcp_mib_field rm_type) argument 836 mptcp_pm_nl_rm_addr_received(struct mptcp_sock *msk) argument 841 mptcp_pm_nl_rm_subflow_received(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) argument 847 mptcp_pm_nl_work(struct mptcp_sock *msk) argument 1061 mptcp_pm_nl_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc) argument 1108 mptcp_pm_nl_subflow_chk_stale(const struct mptcp_sock *msk, struct sock *ssk) argument 1260 struct mptcp_sock *msk; local 1352 mptcp_pm_nl_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id, u8 *flags, int *ifindex) argument 1370 remove_anno_list_by_saddr(struct mptcp_sock *msk, const struct mptcp_addr_info *addr) argument 1385 mptcp_pm_remove_anno_addr(struct mptcp_sock *msk, const struct mptcp_addr_info *addr, bool force) argument 1409 struct mptcp_sock *msk; local 1448 struct mptcp_sock *msk; local 1526 mptcp_pm_remove_addrs(struct mptcp_sock *msk, struct list_head *rm_list) argument 1545 mptcp_pm_remove_addrs_and_subflows(struct mptcp_sock *msk, struct list_head *rm_list) argument 1574 struct mptcp_sock *msk; local 1846 mptcp_pm_nl_fullmesh(struct mptcp_sock *msk, struct mptcp_addr_info *addr) argument 1864 struct mptcp_sock *msk; local 1953 mptcp_userspace_pm_active(const struct mptcp_sock *msk) argument 2009 mptcp_event_put_token_and_ssk(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument 2042 mptcp_event_sub_established(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument 2049 mptcp_event_sub_closed(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument 2071 mptcp_event_created(struct sk_buff *skb, const struct mptcp_sock *msk, const struct sock *ssk) argument 2086 mptcp_event_addr_removed(const struct mptcp_sock *msk, uint8_t id) argument 2121 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 2226 mptcp_event(enum mptcp_event_type type, const struct mptcp_sock *msk, const struct sock *ssk, gfp_t gfp) argument [all...] |
H A D | fastopen.c | 62 void __mptcp_fastopen_gen_msk_ackseq(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, argument 65 struct sock *sk = (struct sock *)msk; 71 pr_debug("msk %p moving seq %llx -> %llx end_seq %llx -> %llx", sk, 72 MPTCP_SKB_CB(skb)->map_seq, MPTCP_SKB_CB(skb)->map_seq + msk->ack_seq, 73 MPTCP_SKB_CB(skb)->end_seq, MPTCP_SKB_CB(skb)->end_seq + msk->ack_seq); 74 MPTCP_SKB_CB(skb)->map_seq += msk->ack_seq; 75 MPTCP_SKB_CB(skb)->end_seq += msk->ack_seq; 78 pr_debug("msk=%p ack_seq=%llx", msk, msk [all...] |
H A D | pm_userspace.c | 11 void mptcp_free_local_addr_list(struct mptcp_sock *msk) argument 14 struct sock *sk = (struct sock *)msk; 17 if (!mptcp_pm_is_userspace(msk)) 20 spin_lock_bh(&msk->pm.lock); 21 list_splice_init(&msk->pm.userspace_pm_local_addr_list, &free_list); 22 spin_unlock_bh(&msk->pm.lock); 29 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, argument 35 struct sock *sk = (struct sock *)msk; 43 spin_lock_bh(&msk->pm.lock); 44 list_for_each_entry(e, &msk 90 mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk, struct mptcp_pm_addr_entry *addr) argument 111 mptcp_userspace_pm_lookup_addr_by_id(struct mptcp_sock *msk, unsigned int id) argument 122 mptcp_userspace_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, unsigned int id, u8 *flags, int *ifindex) argument 139 mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, struct mptcp_addr_info *skc) argument 173 struct mptcp_sock *msk; local 234 mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk, struct genl_info *info) argument 274 struct mptcp_sock *msk; local 339 struct mptcp_sock *msk; local 413 mptcp_nl_find_ssk(struct mptcp_sock *msk, const struct mptcp_addr_info *local, const struct mptcp_addr_info *remote) argument 468 struct mptcp_sock *msk; local 558 struct mptcp_sock *msk; local 617 struct mptcp_sock *msk; local 675 struct mptcp_sock *msk; local [all...] |
H A D | protocol.h | 302 * protected by the msk data lock 353 static inline void msk_owned_by_me(const struct mptcp_sock *msk) argument 355 sock_owned_by_me((const struct sock *)msk); 376 /* the msk socket don't use the backlog, also account for the bulk 396 const struct mptcp_sock *msk = mptcp_sk(sk); local 398 return READ_ONCE(msk->first_pending); 403 struct mptcp_sock *msk = mptcp_sk(sk); local 406 cur = msk->first_pending; 407 return list_is_last(&cur->list, &msk->rtx_queue) ? NULL : 413 const struct mptcp_sock *msk local 426 struct mptcp_sock *msk = mptcp_sk(sk); local 457 struct mptcp_sock *msk; member in struct:mptcp_subflow_request_sock 736 mptcp_data_avail(const struct mptcp_sock *msk) argument 850 mptcp_data_fin_enabled(const struct mptcp_sock *msk) argument 867 const struct mptcp_sock *msk = mptcp_sk(sk); local 1043 mptcp_pm_should_add_signal(struct mptcp_sock *msk) argument 1049 mptcp_pm_should_add_signal_addr(struct mptcp_sock *msk) argument 1054 mptcp_pm_should_add_signal_echo(struct mptcp_sock *msk) argument 1059 mptcp_pm_should_rm_signal(struct mptcp_sock *msk) argument 1064 mptcp_pm_is_userspace(const struct mptcp_sock *msk) argument 1069 mptcp_pm_is_kernel(const struct mptcp_sock *msk) argument 1135 __mptcp_pm_close_subflow(struct mptcp_sock *msk) argument 1141 mptcp_pm_close_subflow(struct mptcp_sock *msk) argument 1158 __mptcp_check_fallback(const struct mptcp_sock *msk) argument 1166 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 1171 __mptcp_do_fallback(struct mptcp_sock *msk) argument 1180 __mptcp_has_initial_subflow(const struct mptcp_sock *msk) argument 1193 struct mptcp_sock *msk; local [all...] |
H A D | token.c | 154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 175 WRITE_ONCE(msk->token, subflow->token); 176 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); 186 * @msk: the just cloned socket linked to the new connection 192 struct mptcp_sock *msk) 195 struct sock *sk = (struct sock *)msk; 206 __sk_nulls_add_node_rcu((struct sock *)msk, &bucket->msk_chain); 214 struct mptcp_sock *msk; local 222 msk = mptcp_sk(sk); 223 if (READ_ONCE(msk 191 mptcp_token_accept(struct mptcp_subflow_request_sock *req, struct mptcp_sock *msk) argument 250 struct mptcp_sock *msk; local 375 mptcp_token_destroy(struct mptcp_sock *msk) argument [all...] |
H A D | subflow.c | 44 if (subflow_req->msk) 45 sock_put((struct sock *)subflow_req->msk); 61 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) argument 63 return mptcp_is_fully_established((void *)msk) && 64 ((mptcp_pm_is_userspace(msk) && 65 mptcp_userspace_pm_active(msk)) || 66 READ_ONCE(msk->pm.accept_subflow)); 72 struct mptcp_sock *msk = subflow_req->msk; local 77 subflow_generate_hmac(READ_ONCE(msk 88 struct mptcp_sock *msk; local 119 subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk) argument 436 subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk) argument 444 struct mptcp_sock *msk = mptcp_sk(sk); local 463 subflow_set_remote_key(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, const struct mptcp_options_received *mp_opt) argument 488 struct mptcp_sock *msk = mptcp_sk(sk); local 514 struct mptcp_sock *msk; local 606 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 729 struct mptcp_sock *msk; local 774 __mptcp_subflow_fully_established(struct mptcp_sock *msk, struct mptcp_subflow_context *subflow, const struct mptcp_options_received *mp_opt) argument 1072 get_mapping_status(struct sock *ssk, struct mptcp_sock *msk) argument 1239 subflow_sched_work_if_closed(struct mptcp_sock *msk, struct sock *ssk) argument 1251 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 1261 mptcp_subflow_fail(struct mptcp_sock *msk, struct sock *ssk) argument 1292 struct mptcp_sock *msk; local 1445 struct mptcp_sock *msk; local 1550 struct mptcp_sock *msk = mptcp_sk(sk); local 1790 struct mptcp_sock *msk; local [all...] |
H A D | syncookies.c | 86 * Look up the saved state based on skb hash & check token matches msk 89 * Caller will check msk can still accept another subflow. The hmac 97 struct mptcp_sock *msk; local 111 msk = mptcp_token_get_sock(net, e->token); 112 if (!msk) { 122 subflow_req->msk = msk;
|
H A D | mptcp_diag.c | 31 struct mptcp_sock *msk = NULL; local 38 msk = mptcp_token_get_sock(net, req->id.idiag_cookie[0]); 39 if (!msk) 43 sk = (struct sock *)msk; 158 struct mptcp_sock *msk; local 166 while ((msk = mptcp_token_iter_next(net, &diag_ctx->s_slot, 168 struct inet_sock *inet = (struct inet_sock *)msk; 169 struct sock *sk = (struct sock *)msk; 202 struct mptcp_sock *msk = mptcp_sk(sk); local 209 struct sock *lsk = READ_ONCE(msk [all...] |
H A D | options.c | 449 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 481 opts->csum_reqd = READ_ONCE(msk->csum_enabled); 562 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 569 opts->csum_reqd = READ_ONCE(msk->csum_enabled); 589 /* passive sockets msk will set the 'can_ack' after accept(), even 593 if (!READ_ONCE(msk->can_ack)) { 598 ack_seq = READ_ONCE(msk->ack_seq); 599 if (READ_ONCE(msk->use_64bit_ack)) { 610 WRITE_ONCE(msk->old_wspace, __mptcp_space((struct sock *)msk)); 655 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 710 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 785 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 830 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 925 check_fully_established(struct mptcp_sock *msk, struct sock *ssk, struct mptcp_subflow_context *subflow, struct sk_buff *skb, struct mptcp_options_received *mp_opt) argument 1031 __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una) argument 1037 ack_update_msk(struct mptcp_sock *msk, struct sock *ssk, struct mptcp_options_received *mp_opt) argument 1079 mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit) argument 1096 add_addr_hmac_valid(struct mptcp_sock *msk, struct mptcp_options_received *mp_opt) argument 1118 struct mptcp_sock *msk = mptcp_sk(subflow->conn); local 1256 struct mptcp_sock *msk; local [all...] |
/linux-master/drivers/net/ethernet/netronome/nfp/flower/ |
H A D | match.c | 12 struct nfp_flower_meta_tci *msk, u8 key_type) 18 msk->nfp_flow_key_layer = key_type; 19 msk->mask_id = ~0; 24 struct nfp_flower_meta_tci *msk, 47 msk->tci |= cpu_to_be16(msk_tci); 53 struct nfp_flower_meta_tci *msk, 57 memset(msk, 0, sizeof(struct nfp_flower_meta_tci)); 59 nfp_flower_compile_meta(ext, msk, key_type); 62 nfp_flower_compile_tci(ext, msk, rule); 96 struct nfp_flower_mac_mpls *msk, 11 nfp_flower_compile_meta(struct nfp_flower_meta_tci *ext, struct nfp_flower_meta_tci *msk, u8 key_type) argument 23 nfp_flower_compile_tci(struct nfp_flower_meta_tci *ext, struct nfp_flower_meta_tci *msk, struct flow_rule *rule) argument 52 nfp_flower_compile_meta_tci(struct nfp_flower_meta_tci *ext, struct nfp_flower_meta_tci *msk, struct flow_rule *rule, u8 key_type, bool qinq_sup) argument 95 nfp_flower_compile_mac(struct nfp_flower_mac_mpls *ext, struct nfp_flower_mac_mpls *msk, struct flow_rule *rule) argument 119 nfp_flower_compile_mpls(struct nfp_flower_mac_mpls *ext, struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, struct netlink_ext_ack *extack) argument 174 nfp_flower_compile_mac_mpls(struct nfp_flower_mac_mpls *ext, struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, struct netlink_ext_ack *extack) argument 188 nfp_flower_compile_tport(struct nfp_flower_tp_ports *ext, struct nfp_flower_tp_ports *msk, struct flow_rule *rule) argument 209 nfp_flower_compile_ip_ext(struct nfp_flower_ip_ext *ext, struct nfp_flower_ip_ext *msk, struct flow_rule *rule) argument 285 nfp_flower_fill_vlan(struct flow_match_vlan *match, struct nfp_flower_vlan *ext, struct nfp_flower_vlan *msk, bool outer_vlan) argument 318 nfp_flower_compile_vlan(struct nfp_flower_vlan *ext, struct nfp_flower_vlan *msk, struct flow_rule *rule) argument 335 nfp_flower_compile_ipv4(struct nfp_flower_ipv4 *ext, struct nfp_flower_ipv4 *msk, struct flow_rule *rule) argument 357 nfp_flower_compile_ipv6(struct nfp_flower_ipv6 *ext, struct nfp_flower_ipv6 *msk, struct flow_rule *rule) argument 385 nfp_flower_compile_geneve_opt(u8 *ext, u8 *msk, struct flow_rule *rule) argument 401 nfp_flower_compile_tun_ipv4_addrs(struct nfp_flower_tun_ipv4 *ext, struct nfp_flower_tun_ipv4 *msk, struct flow_rule *rule) argument 417 nfp_flower_compile_tun_ipv6_addrs(struct nfp_flower_tun_ipv6 *ext, struct nfp_flower_tun_ipv6 *msk, struct flow_rule *rule) argument 438 nfp_flower_compile_tun_ip_ext(struct nfp_flower_tun_ip_ext *ext, struct nfp_flower_tun_ip_ext *msk, struct flow_rule *rule) argument 487 nfp_flower_compile_ipv4_gre_tun(struct nfp_flower_ipv4_gre_tun *ext, struct nfp_flower_ipv4_gre_tun *msk, struct flow_rule *rule) argument 502 nfp_flower_compile_ipv4_udp_tun(struct nfp_flower_ipv4_udp_tun *ext, struct nfp_flower_ipv4_udp_tun *msk, struct flow_rule *rule) argument 512 nfp_flower_compile_ipv6_udp_tun(struct nfp_flower_ipv6_udp_tun *ext, struct nfp_flower_ipv6_udp_tun *msk, struct flow_rule *rule) argument 522 nfp_flower_compile_ipv6_gre_tun(struct nfp_flower_ipv6_gre_tun *ext, struct nfp_flower_ipv6_gre_tun *msk, struct flow_rule *rule) argument 550 u8 *msk; local [all...] |
/linux-master/tools/testing/selftests/bpf/progs/ |
H A D | mptcp_sock.c | 32 struct mptcp_sock *msk; local 60 msk = bpf_skc_to_mptcp_sock(sk); 61 if (!msk) 64 storage = bpf_sk_storage_get(&socket_storage_map, msk, 0, 69 storage->token = msk->token; 70 __builtin_memcpy(storage->ca_name, msk->ca_name, TCP_CA_NAME_MAX); 71 storage->first = msk->first; 81 int BPF_PROG(trace_mptcp_pm_new_connection, struct mptcp_sock *msk, argument 85 token = msk->token;
|
/linux-master/drivers/media/usb/pvrusb2/ |
H A D | pvrusb2-debug.h | 11 #define pvr2_trace(msk, fmt, arg...) do {if (msk & pvrusb2_debug) pr_info("pvrusb2: " fmt "\n", ##arg); } while (0)
|
/linux-master/net/mctp/ |
H A D | af_mctp.c | 55 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local 81 msk->bind_net = smctp->smctp_network; 82 msk->bind_addr = smctp->smctp_addr.s_addr; 83 msk->bind_type = smctp->smctp_type & 0x7f; /* ignore the IC bit */ 98 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local 133 if (msk->addr_ext && addrlen >= sizeof(struct sockaddr_mctp_ext)) { 210 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local 259 if (msk->addr_ext) { 311 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); local 322 msk 332 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); local 424 mctp_ioctl_alloctag(struct mctp_sock *msk, bool tagv2, unsigned long arg) argument 467 mctp_ioctl_droptag(struct mctp_sock *msk, bool tagv2, unsigned long arg) argument 513 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); local 572 struct mctp_sock *msk = container_of(timer, struct mctp_sock, local 614 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local 639 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); local [all...] |
/linux-master/drivers/net/ethernet/aquantia/atlantic/ |
H A D | aq_hw_utils.c | 19 void aq_hw_write_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, argument 22 if (msk ^ ~0) { 26 reg_new = (reg_old & (~msk)) | (val << shift); 35 u32 aq_hw_read_reg_bit(struct aq_hw_s *aq_hw, u32 addr, u32 msk, u32 shift) argument 37 return ((aq_hw_read_reg(aq_hw, addr) & msk) >> shift);
|
/linux-master/kernel/irq/ |
H A D | devres.c | 235 u32 msk; member in struct:irq_generic_chip_devres 244 irq_remove_generic_chip(this->gc, this->msk, this->clr, this->set); 253 * @msk: Bitmask holding the irqs to initialize relative to gc->irq_base 263 u32 msk, enum irq_gc_flags flags, 273 irq_setup_generic_chip(gc, msk, flags, clr, set); 276 dr->msk = msk; 262 devm_irq_setup_generic_chip(struct device *dev, struct irq_chip_generic *gc, u32 msk, enum irq_gc_flags flags, unsigned int clr, unsigned int set) argument
|
H A D | matrix.c | 136 const struct cpumask *msk) 143 for_each_cpu(cpu, msk) { 157 const struct cpumask *msk) 164 for_each_cpu(cpu, msk) { 210 * @msk: On which CPUs the bits should be reserved. 213 * on all CPUs in @msk, but it's not guaranteed that the bits are at the 216 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) argument 220 for_each_cpu(cpu, msk) { 237 for_each_cpu(cpu, msk) { 248 * @msk 135 matrix_find_best_cpu(struct irq_matrix *m, const struct cpumask *msk) argument 156 matrix_find_best_cpu_managed(struct irq_matrix *m, const struct cpumask *msk) argument 257 irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) argument 292 irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, unsigned int *mapped_cpu) argument 383 irq_matrix_alloc(struct irq_matrix *m, const struct cpumask *msk, bool reserved, unsigned int *mapped_cpu) argument [all...] |
/linux-master/drivers/clk/sprd/ |
H A D | pll.c | 54 u32 msk, u32 val) 66 regmap_write(common->regmap, offset, (reg & ~msk) | val); 173 cfg[index].msk = mask; 184 cfg[index].msk |= mask; 189 cfg[index].msk |= mask; 196 cfg[index].msk |= mask; 206 cfg[index].msk |= mask; 214 cfg[index].msk |= mask; 217 if (cfg[i].msk) { 218 sprd_pll_write(pll, i, cfg[i].msk, cf 53 sprd_pll_write(const struct sprd_pll *pll, u8 index, u32 msk, u32 val) argument [all...] |
/linux-master/drivers/usb/mtu3/ |
H A D | mtu3_host.c | 70 u32 reg, msk, val; local 75 msk = WC1_IS_EN | WC1_IS_C(0xf) | WC1_IS_P; 80 msk = WC0_IS_EN | WC0_IS_C(0xf) | WC0_IS_P; 85 msk = WC0_SSUSB0_CDEN | WC0_IS_SPM_EN; 86 val = enable ? msk : 0; 90 msk = WC1_IS_EN_P0_95 | WC1_IS_C_95(0xf) | WC1_IS_P_95; 95 msk = WC0_IS_EN_P2_95 | WC0_IS_C_95(0x7) | WC0_IS_P_95; 100 msk = WC0_IS_EN_P3_95 | WC0_IS_C_95(0x7) | WC0_IS_P_95; 105 msk = SSC_IP_SLEEP_EN | SSC_SPM_INT_EN; 106 val = enable ? msk [all...] |