Home
last modified time | relevance | path

Searched defs:msk (Results 1 – 25 of 201) sorted by relevance

123456789

/kernel/linux/linux-5.10/arch/powerpc/include/asm/
Dfeature-fixups.h39 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
61 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
65 #define END_FTR_SECTION(msk, val) \ argument
68 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
71 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
72 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
76 #define ALT_FTR_SECTION_END_NESTED(msk, val, label) \ argument
78 #define ALT_FTR_SECTION_END_NESTED_IFSET(msk, label) \ argument
80 #define ALT_FTR_SECTION_END_NESTED_IFCLR(msk, label) \ argument
82 #define ALT_FTR_SECTION_END(msk, val) \ argument
[all …]
/kernel/linux/linux-5.10/tools/testing/selftests/powerpc/primitives/asm/
Dfeature-fixups.h39 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
61 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
65 #define END_FTR_SECTION(msk, val) \ argument
68 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
71 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
72 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
76 #define ALT_FTR_SECTION_END_NESTED(msk, val, label) \ argument
78 #define ALT_FTR_SECTION_END_NESTED_IFSET(msk, label) \ argument
80 #define ALT_FTR_SECTION_END_NESTED_IFCLR(msk, label) \ argument
82 #define ALT_FTR_SECTION_END(msk, val) \ argument
[all …]
/kernel/linux/linux-6.6/tools/testing/selftests/powerpc/primitives/asm/
Dfeature-fixups.h57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
77 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
81 #define END_FTR_SECTION(msk, val) \ argument
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
88 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
92 #define ALT_FTR_SECTION_END_NESTED(msk, val, label) \ argument
94 #define ALT_FTR_SECTION_END_NESTED_IFSET(msk, label) \ argument
96 #define ALT_FTR_SECTION_END_NESTED_IFCLR(msk, label) \ argument
98 #define ALT_FTR_SECTION_END(msk, val) \ argument
[all …]
/kernel/linux/linux-6.6/arch/powerpc/include/asm/
Dfeature-fixups.h57 #define MAKE_FTR_SECTION_ENTRY(msk, val, label, sect) \ argument
77 #define END_FTR_SECTION_NESTED(msk, val, label) \ argument
81 #define END_FTR_SECTION(msk, val) \ argument
84 #define END_FTR_SECTION_NESTED_IFSET(msk, label) \ argument
87 #define END_FTR_SECTION_IFSET(msk) END_FTR_SECTION((msk), (msk)) argument
88 #define END_FTR_SECTION_IFCLR(msk) END_FTR_SECTION((msk), 0) argument
92 #define ALT_FTR_SECTION_END_NESTED(msk, val, label) \ argument
94 #define ALT_FTR_SECTION_END_NESTED_IFSET(msk, label) \ argument
96 #define ALT_FTR_SECTION_END_NESTED_IFCLR(msk, label) \ argument
98 #define ALT_FTR_SECTION_END(msk, val) \ argument
[all …]
/kernel/linux/linux-5.10/net/mptcp/
Dpm.c15 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr()
27 int mptcp_pm_remove_addr(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_addr()
36 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, u8 local_id) in mptcp_pm_remove_subflow()
48 void mptcp_pm_new_connection(struct mptcp_sock *msk, int server_side) in mptcp_pm_new_connection()
57 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) in mptcp_pm_allow_new_subflow()
83 static bool mptcp_pm_schedule_work(struct mptcp_sock *msk, in mptcp_pm_schedule_work()
97 void mptcp_pm_fully_established(struct mptcp_sock *msk) in mptcp_pm_fully_established()
115 void mptcp_pm_connection_closed(struct mptcp_sock *msk) in mptcp_pm_connection_closed()
120 void mptcp_pm_subflow_established(struct mptcp_sock *msk, in mptcp_pm_subflow_established()
138 void mptcp_pm_subflow_closed(struct mptcp_sock *msk, u8 id) in mptcp_pm_subflow_closed()
[all …]
Dprotocol.c29 struct mptcp_sock msk; member
48 static struct socket *__mptcp_nmpc_socket(const struct mptcp_sock *msk) in __mptcp_nmpc_socket()
80 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback()
90 static int __mptcp_socket_create(struct mptcp_sock *msk) in __mptcp_socket_create()
141 static bool mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to, in mptcp_ooo_try_coalesce()
154 static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb) in mptcp_data_queue_ofo()
264 static bool __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk, in __mptcp_move_skb()
330 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_check_data_fin_ack() local
365 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin() local
395 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_check_data_fin() local
[all …]
Dpm_netlink.c133 struct mptcp_sock *msk) in select_local_address()
182 static void check_work_pending(struct mptcp_sock *msk) in check_work_pending()
191 lookup_anno_list_by_saddr(struct mptcp_sock *msk, in lookup_anno_list_by_saddr()
207 struct mptcp_sock *msk = entry->sock; in mptcp_pm_add_timer() local
244 mptcp_pm_del_add_timer(struct mptcp_sock *msk, in mptcp_pm_del_add_timer()
262 static bool mptcp_pm_alloc_anno_list(struct mptcp_sock *msk, in mptcp_pm_alloc_anno_list()
287 void mptcp_pm_free_anno_list(struct mptcp_sock *msk) in mptcp_pm_free_anno_list()
305 static void mptcp_pm_create_subflow_or_signal_addr(struct mptcp_sock *msk) in mptcp_pm_create_subflow_or_signal_addr()
359 void mptcp_pm_nl_fully_established(struct mptcp_sock *msk) in mptcp_pm_nl_fully_established()
364 void mptcp_pm_nl_subflow_established(struct mptcp_sock *msk) in mptcp_pm_nl_subflow_established()
[all …]
Dtoken_test.c54 struct mptcp_sock *msk; in build_msk() local
67 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() local
89 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_accept() local
108 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_destroyed() local
Doptions.c490 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() local
585 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() local
633 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr() local
724 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk, in check_fully_established()
815 static void update_una(struct mptcp_sock *msk, in update_una()
842 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit) in mptcp_update_rcv_data_fin()
859 static bool add_addr_hmac_valid(struct mptcp_sock *msk, in add_addr_hmac_valid()
888 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_incoming_options() local
Dtoken.c155 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() local
191 struct mptcp_sock *msk) in mptcp_token_accept()
211 struct mptcp_sock *msk; in mptcp_token_exists() local
247 struct mptcp_sock *msk; in mptcp_token_get_sock() local
372 void mptcp_token_destroy(struct mptcp_sock *msk) in mptcp_token_destroy()
Dmptcp_diag.c32 struct mptcp_sock *msk = NULL; in mptcp_diag_dump_one() local
77 struct mptcp_sock *msk; in mptcp_diag_dump() local
116 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_diag_get_info() local
/kernel/linux/linux-6.6/net/mptcp/
Dpm.c17 int mptcp_pm_announce_addr(struct mptcp_sock *msk, in mptcp_pm_announce_addr()
45 int mptcp_pm_remove_addr(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) in mptcp_pm_remove_addr()
64 int mptcp_pm_remove_subflow(struct mptcp_sock *msk, const struct mptcp_rm_list *rm_list) in mptcp_pm_remove_subflow()
76 void mptcp_pm_new_connection(struct mptcp_sock *msk, const struct sock *ssk, int server_side) in mptcp_pm_new_connection()
86 bool mptcp_pm_allow_new_subflow(struct mptcp_sock *msk) in mptcp_pm_allow_new_subflow()
125 static bool mptcp_pm_schedule_work(struct mptcp_sock *msk, in mptcp_pm_schedule_work()
138 void mptcp_pm_fully_established(struct mptcp_sock *msk, const struct sock *ssk) in mptcp_pm_fully_established()
165 void mptcp_pm_connection_closed(struct mptcp_sock *msk) in mptcp_pm_connection_closed()
170 void mptcp_pm_subflow_established(struct mptcp_sock *msk) in mptcp_pm_subflow_established()
187 void mptcp_pm_subflow_check_next(struct mptcp_sock *msk, const struct sock *ssk, in mptcp_pm_subflow_check_next()
[all …]
Dsockopt.c20 static struct sock *__mptcp_tcp_fallback(struct mptcp_sock *msk) in __mptcp_tcp_fallback()
51 static void sockopt_seq_inc(struct mptcp_sock *msk) in sockopt_seq_inc()
58 static int mptcp_get_int_option(struct mptcp_sock *msk, sockptr_t optval, in mptcp_get_int_option()
70 static void mptcp_sol_socket_sync_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_sync_intval()
123 static int mptcp_sol_socket_intval(struct mptcp_sock *msk, int optname, int val) in mptcp_sol_socket_intval()
138 static void mptcp_so_incoming_cpu(struct mptcp_sock *msk, int val) in mptcp_so_incoming_cpu()
147 static int mptcp_setsockopt_sol_socket_tstamp(struct mptcp_sock *msk, int optname, int val) in mptcp_setsockopt_sol_socket_tstamp()
172 static int mptcp_setsockopt_sol_socket_int(struct mptcp_sock *msk, int optname, in mptcp_setsockopt_sol_socket_int()
207 static int mptcp_setsockopt_sol_socket_timestamping(struct mptcp_sock *msk, in mptcp_setsockopt_sol_socket_timestamping()
251 static int mptcp_setsockopt_sol_socket_linger(struct mptcp_sock *msk, sockptr_t optval, in mptcp_setsockopt_sol_socket_linger()
[all …]
Dprotocol.c34 struct mptcp_sock msk; member
53 static u64 mptcp_wnd_end(const struct mptcp_sock *msk) in mptcp_wnd_end()
82 static int __mptcp_socket_create(struct mptcp_sock *msk) in __mptcp_socket_create()
112 struct sock *__mptcp_nmpc_sk(struct mptcp_sock *msk) in __mptcp_nmpc_sk()
174 static bool mptcp_ooo_try_coalesce(struct mptcp_sock *msk, struct sk_buff *to, in mptcp_ooo_try_coalesce()
192 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_uncharge() local
225 static void mptcp_data_queue_ofo(struct mptcp_sock *msk, struct sk_buff *skb) in mptcp_data_queue_ofo()
338 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_rmem_schedule() local
354 static bool __mptcp_move_skb(struct mptcp_sock *msk, struct sock *ssk, in __mptcp_move_skb()
431 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_pending_data_fin_ack() local
[all …]
Dpm_netlink.c57 pm_nl_get_pernet_from_msk(const struct mptcp_sock *msk) in pm_nl_get_pernet_from_msk()
153 const struct mptcp_sock *msk) in select_local_address()
175 select_signal_address(struct pm_nl_pernet *pernet, const struct mptcp_sock *msk) in select_signal_address()
199 unsigned int mptcp_pm_get_add_addr_signal_max(const struct mptcp_sock *msk) in mptcp_pm_get_add_addr_signal_max()
207 unsigned int mptcp_pm_get_add_addr_accept_max(const struct mptcp_sock *msk) in mptcp_pm_get_add_addr_accept_max()
215 unsigned int mptcp_pm_get_subflows_max(const struct mptcp_sock *msk) in mptcp_pm_get_subflows_max()
223 unsigned int mptcp_pm_get_local_addr_max(const struct mptcp_sock *msk) in mptcp_pm_get_local_addr_max()
231 bool mptcp_pm_nl_check_work_pending(struct mptcp_sock *msk) in mptcp_pm_nl_check_work_pending()
245 mptcp_lookup_anno_list_by_saddr(const struct mptcp_sock *msk, in mptcp_lookup_anno_list_by_saddr()
260 bool mptcp_pm_sport_in_anno_list(struct mptcp_sock *msk, const struct sock *sk) in mptcp_pm_sport_in_anno_list()
[all …]
Dpm_userspace.c10 void mptcp_free_local_addr_list(struct mptcp_sock *msk) in mptcp_free_local_addr_list()
28 static int mptcp_userspace_pm_append_new_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_append_new_local_addr()
89 static int mptcp_userspace_pm_delete_local_addr(struct mptcp_sock *msk, in mptcp_userspace_pm_delete_local_addr()
109 int mptcp_userspace_pm_get_flags_and_ifindex_by_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_flags_and_ifindex_by_id()
131 int mptcp_userspace_pm_get_local_id(struct mptcp_sock *msk, in mptcp_userspace_pm_get_local_id()
165 struct mptcp_sock *msk; in mptcp_nl_cmd_announce() local
223 static int mptcp_userspace_pm_remove_id_zero_address(struct mptcp_sock *msk, in mptcp_userspace_pm_remove_id_zero_address()
263 struct mptcp_sock *msk; in mptcp_nl_cmd_remove() local
332 struct mptcp_sock *msk; in mptcp_nl_cmd_sf_create() local
400 static struct sock *mptcp_nl_find_ssk(struct mptcp_sock *msk, in mptcp_nl_find_ssk()
[all …]
Dsched.c19 static int mptcp_sched_default_get_subflow(struct mptcp_sock *msk, in mptcp_sched_default_get_subflow()
86 int mptcp_init_sched(struct mptcp_sock *msk, in mptcp_init_sched()
104 void mptcp_release_sched(struct mptcp_sock *msk) in mptcp_release_sched()
124 int mptcp_sched_get_send(struct mptcp_sock *msk) in mptcp_sched_get_send()
153 int mptcp_sched_get_retrans(struct mptcp_sock *msk) in mptcp_sched_get_retrans()
Doptions.c449 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_mp() local
562 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_dss() local
655 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_add_addr() local
710 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_rm_addr() local
785 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options_fastclose() local
830 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_established_options() local
925 static bool check_fully_established(struct mptcp_sock *msk, struct sock *ssk, in check_fully_established()
1031 static void __mptcp_snd_una_update(struct mptcp_sock *msk, u64 new_snd_una) in __mptcp_snd_una_update()
1037 static void ack_update_msk(struct mptcp_sock *msk, in ack_update_msk()
1078 bool mptcp_update_rcv_data_fin(struct mptcp_sock *msk, u64 data_fin_seq, bool use_64bit) in mptcp_update_rcv_data_fin()
[all …]
Dtoken_test.c54 struct mptcp_sock *msk; in build_msk() local
70 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_msk_basic() local
92 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_accept() local
111 struct mptcp_sock *msk = build_msk(test); in mptcp_token_test_destroyed() local
Dsubflow.c62 static bool mptcp_can_accept_new_subflow(const struct mptcp_sock *msk) in mptcp_can_accept_new_subflow()
73 struct mptcp_sock *msk = subflow_req->msk; in subflow_req_create_thmac() local
88 struct mptcp_sock *msk; in subflow_token_join_request() local
119 static bool subflow_use_different_sport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_sport()
417 static bool subflow_use_different_dport(struct mptcp_sock *msk, const struct sock *sk) in subflow_use_different_dport()
425 struct mptcp_sock *msk = mptcp_sk(sk); in __mptcp_sync_state() local
444 static void subflow_set_remote_key(struct mptcp_sock *msk, in subflow_set_remote_key()
469 struct mptcp_sock *msk = mptcp_sk(sk); in mptcp_propagate_state() local
495 struct mptcp_sock *msk; in subflow_finish_connect() local
587 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in subflow_chk_local_id() local
[all …]
Dtoken.c154 struct mptcp_sock *msk = mptcp_sk(subflow->conn); in mptcp_token_new_connect() local
192 struct mptcp_sock *msk) in mptcp_token_accept()
214 struct mptcp_sock *msk; in mptcp_token_exists() local
250 struct mptcp_sock *msk; in mptcp_token_get_sock() local
375 void mptcp_token_destroy(struct mptcp_sock *msk) in mptcp_token_destroy()
/kernel/linux/linux-6.6/drivers/net/ethernet/netronome/nfp/flower/
Dmatch.c12 struct nfp_flower_meta_tci *msk, u8 key_type) in nfp_flower_compile_meta()
24 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_tci()
53 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_meta_tci()
96 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mac()
120 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mpls()
175 struct nfp_flower_mac_mpls *msk, in nfp_flower_compile_mac_mpls()
189 struct nfp_flower_tp_ports *msk, in nfp_flower_compile_tport()
210 struct nfp_flower_ip_ext *msk, struct flow_rule *rule) in nfp_flower_compile_ip_ext()
287 struct nfp_flower_vlan *msk, bool outer_vlan) in nfp_flower_fill_vlan()
319 struct nfp_flower_vlan *msk, in nfp_flower_compile_vlan()
[all …]
/kernel/linux/linux-5.10/drivers/net/ethernet/netronome/nfp/flower/
Dmatch.c12 struct nfp_flower_meta_tci *msk, in nfp_flower_compile_meta_tci()
79 struct nfp_flower_mac_mpls *msk, struct flow_rule *rule, in nfp_flower_compile_mac()
145 struct nfp_flower_tp_ports *msk, in nfp_flower_compile_tport()
164 struct nfp_flower_ip_ext *msk, struct flow_rule *rule) in nfp_flower_compile_ip_ext()
257 struct nfp_flower_vlan *msk, in nfp_flower_compile_vlan()
279 struct nfp_flower_ipv4 *msk, struct flow_rule *rule) in nfp_flower_compile_ipv4()
299 struct nfp_flower_ipv6 *msk, struct flow_rule *rule) in nfp_flower_compile_ipv6()
318 nfp_flower_compile_geneve_opt(void *ext, void *msk, struct flow_rule *rule) in nfp_flower_compile_geneve_opt()
331 struct nfp_flower_tun_ipv4 *msk, in nfp_flower_compile_tun_ipv4_addrs()
347 struct nfp_flower_tun_ipv6 *msk, in nfp_flower_compile_tun_ipv6_addrs()
[all …]
/kernel/linux/linux-6.6/net/mctp/
Daf_mctp.c55 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_bind() local
98 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_sendmsg() local
210 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_recvmsg() local
311 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); in mctp_setsockopt() local
332 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); in mctp_getsockopt() local
353 static int mctp_ioctl_alloctag(struct mctp_sock *msk, unsigned long arg) in mctp_ioctl_alloctag()
395 static int mctp_ioctl_droptag(struct mctp_sock *msk, unsigned long arg) in mctp_ioctl_droptag()
441 struct mctp_sock *msk = container_of(sock->sk, struct mctp_sock, sk); in mctp_ioctl() local
495 struct mctp_sock *msk = container_of(timer, struct mctp_sock, in mctp_sk_expire_keys() local
537 struct mctp_sock *msk = container_of(sk, struct mctp_sock, sk); in mctp_sk_init() local
[all …]
/kernel/linux/linux-6.6/kernel/irq/
Dmatrix.c130 const struct cpumask *msk) in matrix_find_best_cpu()
151 const struct cpumask *msk) in matrix_find_best_cpu_managed()
210 int irq_matrix_reserve_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_reserve_managed()
251 void irq_matrix_remove_managed(struct irq_matrix *m, const struct cpumask *msk) in irq_matrix_remove_managed()
286 int irq_matrix_alloc_managed(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc_managed()
377 int irq_matrix_alloc(struct irq_matrix *m, const struct cpumask *msk, in irq_matrix_alloc()

123456789