Home
last modified time | relevance | path

Searched refs:nc (Results 1 – 25 of 200) sorted by relevance

12345678

/freebsd/contrib/llvm-project/clang/include/clang/Basic/
H A DBuiltinsMips.def29 BUILTIN(__builtin_mips_madd, "LLiLLiii", "nc")
30 BUILTIN(__builtin_mips_maddu, "LLiLLiUiUi", "nc")
31 BUILTIN(__builtin_mips_msub, "LLiLLiii", "nc")
32 BUILTIN(__builtin_mips_msubu, "LLiLLiUiUi", "nc")
40 BUILTIN(__builtin_mips_modsub, "iii", "nc")
42 BUILTIN(__builtin_mips_raddu_w_qb, "iV4Sc", "nc")
47 BUILTIN(__builtin_mips_precrq_qb_ph, "V4ScV2sV2s", "nc")
49 BUILTIN(__builtin_mips_precrq_ph_w, "V2sii", "nc")
51 BUILTIN(__builtin_mips_preceq_w_phl, "iV2s", "nc")
52 BUILTIN(__builtin_mips_preceq_w_phr, "iV2s", "nc")
[all …]
H A DBuiltinsLoongArchLASX.def15 TARGET_BUILTIN(__builtin_lasx_xvadd_b, "V32ScV32ScV32Sc", "nc", "lasx")
16 TARGET_BUILTIN(__builtin_lasx_xvadd_h, "V16sV16sV16s", "nc", "lasx")
17 TARGET_BUILTIN(__builtin_lasx_xvadd_w, "V8iV8iV8i", "nc", "lasx")
18 TARGET_BUILTIN(__builtin_lasx_xvadd_d, "V4LLiV4LLiV4LLi", "nc", "lasx")
19 TARGET_BUILTIN(__builtin_lasx_xvadd_q, "V4LLiV4LLiV4LLi", "nc", "lasx")
21 TARGET_BUILTIN(__builtin_lasx_xvsub_b, "V32ScV32ScV32Sc", "nc", "lasx")
22 TARGET_BUILTIN(__builtin_lasx_xvsub_h, "V16sV16sV16s", "nc", "lasx")
23 TARGET_BUILTIN(__builtin_lasx_xvsub_w, "V8iV8iV8i", "nc", "lasx")
24 TARGET_BUILTIN(__builtin_lasx_xvsub_d, "V4LLiV4LLiV4LLi", "nc", "lasx")
25 TARGET_BUILTIN(__builtin_lasx_xvsub_q, "V4LLiV4LLiV4LLi", "nc", "lasx")
[all …]
H A DBuiltinsLoongArchLSX.def15 TARGET_BUILTIN(__builtin_lsx_vadd_b, "V16ScV16ScV16Sc", "nc", "lsx")
16 TARGET_BUILTIN(__builtin_lsx_vadd_h, "V8sV8sV8s", "nc", "lsx")
17 TARGET_BUILTIN(__builtin_lsx_vadd_w, "V4iV4iV4i", "nc", "lsx")
18 TARGET_BUILTIN(__builtin_lsx_vadd_d, "V2LLiV2LLiV2LLi", "nc", "lsx")
19 TARGET_BUILTIN(__builtin_lsx_vadd_q, "V2LLiV2LLiV2LLi", "nc", "lsx")
21 TARGET_BUILTIN(__builtin_lsx_vsub_b, "V16ScV16ScV16Sc", "nc", "lsx")
22 TARGET_BUILTIN(__builtin_lsx_vsub_h, "V8sV8sV8s", "nc", "lsx")
23 TARGET_BUILTIN(__builtin_lsx_vsub_w, "V4iV4iV4i", "nc", "lsx")
24 TARGET_BUILTIN(__builtin_lsx_vsub_d, "V2LLiV2LLiV2LLi", "nc", "lsx")
25 TARGET_BUILTIN(__builtin_lsx_vsub_q, "V2LLiV2LLiV2LLi", "nc", "lsx")
[all …]
H A DBuiltinsAMDGPU.def28 BUILTIN(__builtin_amdgcn_dispatch_ptr, "v*4", "nc")
29 BUILTIN(__builtin_amdgcn_kernarg_segment_ptr, "v*4", "nc")
30 BUILTIN(__builtin_amdgcn_implicitarg_ptr, "v*4", "nc")
31 BUILTIN(__builtin_amdgcn_queue_ptr, "v*4", "nc")
33 BUILTIN(__builtin_amdgcn_workgroup_id_x, "Ui", "nc")
34 BUILTIN(__builtin_amdgcn_workgroup_id_y, "Ui", "nc")
35 BUILTIN(__builtin_amdgcn_workgroup_id_z, "Ui", "nc")
37 BUILTIN(__builtin_amdgcn_workitem_id_x, "Ui", "nc")
38 BUILTIN(__builtin_amdgcn_workitem_id_y, "Ui", "nc")
39 BUILTIN(__builtin_amdgcn_workitem_id_z, "Ui", "nc")
[all …]
H A DBuiltinsWebAssembly.def29 TARGET_BUILTIN(__builtin_wasm_tls_size, "z", "nc", "bulk-memory")
30 TARGET_BUILTIN(__builtin_wasm_tls_align, "z", "nc", "bulk-memory")
34 BUILTIN(__builtin_wasm_min_f32, "fff", "nc")
35 BUILTIN(__builtin_wasm_max_f32, "fff", "nc")
36 BUILTIN(__builtin_wasm_min_f64, "ddd", "nc")
37 BUILTIN(__builtin_wasm_max_f64, "ddd", "nc")
49 BUILTIN(__builtin_wasm_trunc_s_i32_f32, "if", "nc")
50 BUILTIN(__builtin_wasm_trunc_u_i32_f32, "if", "nc")
51 BUILTIN(__builtin_wasm_trunc_s_i32_f64, "id", "nc")
52 BUILTIN(__builtin_wasm_trunc_u_i32_f64, "id", "nc")
[all …]
H A DBuiltinsARM.def32 BUILTIN(__builtin_arm_smulbb, "iii", "nc")
33 BUILTIN(__builtin_arm_smulbt, "iii", "nc")
34 BUILTIN(__builtin_arm_smultb, "iii", "nc")
35 BUILTIN(__builtin_arm_smultt, "iii", "nc")
36 BUILTIN(__builtin_arm_smulwb, "iii", "nc")
37 BUILTIN(__builtin_arm_smulwt, "iii", "nc")
40 BUILTIN(__builtin_arm_qadd, "iii", "nc")
41 BUILTIN(__builtin_arm_qsub, "iii", "nc")
42 BUILTIN(__builtin_arm_qdbl, "ii", "nc")
43 BUILTIN(__builtin_arm_ssat, "iiUi", "nc")
[all …]
H A DBuiltinsAArch64.def38 BUILTIN(__builtin_arm_rbit, "UiUi", "nc")
39 BUILTIN(__builtin_arm_rbit64, "WUiWUi", "nc")
40 BUILTIN(__builtin_arm_cls, "UiZUi", "nc")
41 BUILTIN(__builtin_arm_cls64, "UiWUi", "nc")
42 BUILTIN(__builtin_arm_clz, "UiZUi", "nc")
43 BUILTIN(__builtin_arm_clz64, "UiWUi", "nc")
58 TARGET_BUILTIN(__builtin_arm_crc32b, "UiUiUc", "nc", "crc")
59 TARGET_BUILTIN(__builtin_arm_crc32cb, "UiUiUc", "nc", "crc")
60 TARGET_BUILTIN(__builtin_arm_crc32h, "UiUiUs", "nc", "crc")
61 TARGET_BUILTIN(__builtin_arm_crc32ch, "UiUiUs", "nc", "crc")
[all …]
/freebsd/sys/dev/ntb/
H A Dntb.c63 struct ntb_child *nc; in ntb_register_device() local
100 nc = malloc(sizeof(*nc), M_DEVBUF, M_WAITOK | M_ZERO); in ntb_register_device()
101 nc->function = i; in ntb_register_device()
102 nc->mwoff = mwu; in ntb_register_device()
103 nc->mwcnt = mw; in ntb_register_device()
104 nc->spadoff = spadu; in ntb_register_device()
105 nc->spadcnt = spad; in ntb_register_device()
106 nc->dboff = dbu; in ntb_register_device()
107 nc->dbcnt = db; in ntb_register_device()
108 nc->dbmask = (db == 0) ? 0 : (0xffffffffffffffff >> (64 - db)); in ntb_register_device()
[all …]
/freebsd/lib/libnvmf/
H A Dnvmf_transport.c113 struct nvmf_capsule *nc, *tc; in nvmf_free_qpair() local
115 TAILQ_FOREACH_SAFE(nc, &qp->nq_rx_capsules, nc_link, tc) { in nvmf_free_qpair()
116 TAILQ_REMOVE(&qp->nq_rx_capsules, nc, nc_link); in nvmf_free_qpair()
117 nvmf_free_capsule(nc); in nvmf_free_qpair()
127 struct nvmf_capsule *nc; in nvmf_allocate_command() local
129 nc = qp->nq_association->na_ops->allocate_capsule(qp); in nvmf_allocate_command()
130 if (nc == NULL) in nvmf_allocate_command()
133 nc->nc_qpair = qp; in nvmf_allocate_command()
134 nc->nc_qe_len = sizeof(struct nvme_command); in nvmf_allocate_command()
135 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command()
[all …]
H A Dnvmf_tcp.c55 struct nvmf_capsule nc; member
81 #define TASSOC(nc) ((struct nvmf_tcp_association *)(na)) argument
82 #define TCAP(nc) ((struct nvmf_tcp_capsule *)(nc)) argument
83 #define CTCAP(nc) ((const struct nvmf_tcp_capsule *)(nc)) argument
373 struct nvmf_capsule *nc; in nvmf_tcp_save_command_capsule() local
378 nc = nvmf_allocate_command(&qp->qp, &cmd->ccsqe); in nvmf_tcp_save_command_capsule()
379 if (nc == NULL) in nvmf_tcp_save_command_capsule()
382 tc = TCAP(nc); in nvmf_tcp_save_command_capsule()
394 struct nvmf_capsule *nc; in nvmf_tcp_save_response_capsule() local
399 nc = nvmf_allocate_response(&qp->qp, &rsp->rccqe); in nvmf_tcp_save_response_capsule()
[all …]
H A Dlibnvmf.h103 void nvmf_free_capsule(struct nvmf_capsule *nc);
104 int nvmf_capsule_append_data(struct nvmf_capsule *nc,
106 int nvmf_transmit_capsule(struct nvmf_capsule *nc);
108 const void *nvmf_capsule_sqe(const struct nvmf_capsule *nc);
109 const void *nvmf_capsule_cqe(const struct nvmf_capsule *nc);
125 uint8_t nvmf_validate_command_capsule(const struct nvmf_capsule *nc);
140 int nvmf_receive_controller_data(const struct nvmf_capsule *nc,
150 int nvmf_send_controller_data(const struct nvmf_capsule *nc,
158 void nvmf_init_cqe(void *cqe, const struct nvmf_capsule *nc,
165 int nvmf_send_response(const struct nvmf_capsule *nc, const void *cqe);
[all …]
H A Dnvmf_controller.c19 nvmf_init_cqe(void *cqe, const struct nvmf_capsule *nc, uint16_t status) in nvmf_init_cqe() argument
22 const struct nvme_command *cmd = nvmf_capsule_sqe(nc); in nvmf_init_cqe()
30 nvmf_simple_response(const struct nvmf_capsule *nc, uint8_t sc_type, in nvmf_simple_response() argument
38 nvmf_init_cqe(&cpl, nc, status); in nvmf_simple_response()
39 return (nvmf_allocate_response(nc->nc_qpair, &cpl)); in nvmf_simple_response()
46 struct nvmf_capsule *nc; in nvmf_controller_receive_capsule() local
51 error = nvmf_receive_capsule(qp, &nc); in nvmf_controller_receive_capsule()
55 sc_status = nvmf_validate_command_capsule(nc); in nvmf_controller_receive_capsule()
57 nvmf_send_generic_error(nc, sc_status); in nvmf_controller_receive_capsule()
58 nvmf_free_capsule(nc); in nvmf_controller_receive_capsule()
[all …]
/freebsd/sys/dev/nvmf/
H A Dnvmf_transport.c97 struct nvmf_capsule *nc; in nvmf_allocate_command() local
101 nc = qp->nq_ops->allocate_capsule(qp, how); in nvmf_allocate_command()
102 if (nc == NULL) in nvmf_allocate_command()
105 nc->nc_qpair = qp; in nvmf_allocate_command()
106 nc->nc_qe_len = sizeof(struct nvme_command); in nvmf_allocate_command()
107 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command()
110 nc->nc_sqe.fuse &= ~NVMEM(NVME_CMD_PSDT); in nvmf_allocate_command()
111 nc->nc_sqe.fuse |= NVMEF(NVME_CMD_PSDT, NVME_PSDT_SGL); in nvmf_allocate_command()
112 return (nc); in nvmf_allocate_command()
118 struct nvmf_capsule *nc; in nvmf_allocate_response() local
[all …]
H A Dnvmf_transport.h74 void nvmf_free_capsule(struct nvmf_capsule *nc);
75 int nvmf_capsule_append_data(struct nvmf_capsule *nc,
78 int nvmf_transmit_capsule(struct nvmf_capsule *nc);
79 void nvmf_abort_capsule_data(struct nvmf_capsule *nc, int error);
80 void *nvmf_capsule_sqe(struct nvmf_capsule *nc);
81 void *nvmf_capsule_cqe(struct nvmf_capsule *nc);
82 bool nvmf_sqhd_valid(struct nvmf_capsule *nc);
92 uint8_t nvmf_validate_command_capsule(struct nvmf_capsule *nc);
110 int nvmf_receive_controller_data(struct nvmf_capsule *nc,
136 u_int nvmf_send_controller_data(struct nvmf_capsule *nc,
H A Dnvmf_transport_internal.h31 void (*free_capsule)(struct nvmf_capsule *nc);
32 int (*transmit_capsule)(struct nvmf_capsule *nc);
33 uint8_t (*validate_command_capsule)(struct nvmf_capsule *nc);
36 size_t (*capsule_data_len)(const struct nvmf_capsule *nc);
37 int (*receive_controller_data)(struct nvmf_capsule *nc,
39 u_int (*send_controller_data)(struct nvmf_capsule *nc,
106 nvmf_capsule_received(struct nvmf_qpair *nq, struct nvmf_capsule *nc) in nvmf_capsule_received() argument
108 nq->nq_receive(nq->nq_receive_arg, nc); in nvmf_capsule_received()
H A Dnvmf_tcp.c118 struct nvmf_capsule nc; member
133 #define TCAP(nc) ((struct nvmf_tcp_capsule *)(nc)) argument
387 struct nvmf_capsule *nc; in nvmf_tcp_save_command_capsule() local
392 nc = nvmf_allocate_command(&qp->qp, &cmd->ccsqe, M_WAITOK); in nvmf_tcp_save_command_capsule()
394 tc = TCAP(nc); in nvmf_tcp_save_command_capsule()
397 nvmf_capsule_received(&qp->qp, nc); in nvmf_tcp_save_command_capsule()
406 struct nvmf_capsule *nc; in nvmf_tcp_save_response_capsule() local
411 nc = nvmf_allocate_response(&qp->qp, &rsp->rccqe, M_WAITOK); in nvmf_tcp_save_response_capsule()
413 nc->nc_sqhd_valid = true; in nvmf_tcp_save_response_capsule()
414 tc = TCAP(nc); in nvmf_tcp_save_response_capsule()
[all …]
/freebsd/usr.sbin/nvmfd/
H A Dcontroller.c61 handle_property_get(const struct controller *c, const struct nvmf_capsule *nc, in handle_property_get() argument
66 nvmf_init_cqe(&rsp, nc, 0); in handle_property_get()
93 nvmf_send_response(nc, &rsp); in handle_property_get()
96 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_property_get()
100 handle_property_set(struct controller *c, const struct nvmf_capsule *nc, in handle_property_set() argument
114 nvmf_send_success(nc); in handle_property_set()
117 nvmf_send_generic_error(nc, NVME_SC_INVALID_FIELD); in handle_property_set()
122 const struct nvmf_capsule *nc, const struct nvmf_fabric_cmd *fc) in handle_fabrics_command() argument
126 handle_property_get(c, nc, in handle_fabrics_command()
130 handle_property_set(c, nc, in handle_fabrics_command()
[all …]
/freebsd/tools/diag/dumpvfscache/
H A Ddumpvfscache.c72 struct namecache *nc; in main() local
84 nc = malloc(sizeof *nc + NAME_MAX); in main()
97 kvm_read(kvm, p, nc, sizeof *nc + NAME_MAX); in main()
98 kvm_read(kvm, (u_long)nc->nc_dvp, &vn, sizeof vn); in main()
99 nc->nc_name[nc->nc_nlen] = '\0'; in main()
100 for (j=k=kn=0;nc->nc_name[j];j++) { in main()
101 k+= nc->nc_name[j]; in main()
103 kn+= nc->nc_name[j]; in main()
108 kn = wlpsacrc(nc->nc_name,nc->nc_nlen); in main()
117 i,nc->nc_dvp, k, nc->nc_vp, vn.v_id, nc->nc_name); in main()
[all …]
/freebsd/sys/dev/nvmf/controller/
H A Dnvmft_controller.c537 struct nvmf_capsule *nc, const struct nvme_command *cmd) in handle_get_log_page() argument
566 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
593 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
610 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
633 status = nvmf_send_controller_data(nc, 0, m, len); in handle_get_log_page()
645 nvmft_command_completed(ctrlr->admin, nc); in handle_get_log_page()
647 nvmft_send_generic_error(ctrlr->admin, nc, status); in handle_get_log_page()
648 nvmf_free_capsule(nc); in handle_get_log_page()
659 struct nvmf_capsule *nc, const struct nvme_command *cmd) in handle_identify_command() argument
667 data_len = nvmf_capsule_data_len(nc); in handle_identify_command()
[all …]
H A Dnvmft_qpair.c45 struct nvmf_capsule *nc, uint8_t sc_status);
68 nvmft_receive_capsule(void *arg, struct nvmf_capsule *nc) in nvmft_receive_capsule() argument
75 cmd = nvmf_capsule_sqe(nc); in nvmft_receive_capsule()
79 nvmf_free_capsule(nc); in nvmft_receive_capsule()
83 sc_status = nvmf_validate_command_capsule(nc); in nvmft_receive_capsule()
85 _nvmft_send_generic_error(qp, nc, sc_status); in nvmft_receive_capsule()
86 nvmf_free_capsule(nc); in nvmft_receive_capsule()
92 _nvmft_send_generic_error(qp, nc, NVME_SC_COMMAND_ID_CONFLICT); in nvmft_receive_capsule()
93 nvmf_free_capsule(nc); in nvmft_receive_capsule()
98 nvmft_handle_admin_command(ctrlr, nc); in nvmft_receive_capsule()
[all …]
/freebsd/sbin/bsdlabel/
H A Ddisktab25 :ty=floppy:se#512:nt#2:rm#300:ns#9:nc#40:\
30 :ty=floppy:se#512:nt#2:rm#300:ns#9:nc#80:\
35 :ty=floppy:se#512:nt#2:rm#360:ns#15:nc#80:\
40 :ty=floppy:se#512:nt#2:rm#300:ns#18:nc#80:\
45 :ty=floppy:se#512:nt#2:rm#300:ns#36:nc#80:\
55 :ty=floppy:se#512:nt#2:rm#300:ns#10:nc#80:\
60 :ty=floppy:se#512:nt#2:rm#300:ns#10:nc#82:\
65 :ty=floppy:se#512:nt#2:rm#300:ns#18:nc#82:\
70 :ty=floppy:se#512:nt#2:rm#300:ns#21:nc#82:\
78 :ty=floppy:se#512:nt#8:rm#300:ns#32:nc#963:\
[all …]
/freebsd/tests/sys/netpfil/pf/
H A Dsctp.sh65 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
70 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1234)
81 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 &
84 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1234)
90 echo "foo" | jexec ${j}a nc --sctp -N -l 1235 &
93 out=$(jexec ${j}b nc --sctp -N -w 3 192.0.2.1 1235)
99 out=$(jexec ${j}b nc --sctp -N -w 3 -p 1234 192.0.2.1 1235)
139 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 &
144 out=$(jexec ${j}b nc --sctp -N -w 3 2001:db8::a 1234)
155 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 &
[all …]
/freebsd/contrib/mandoc/
H A Dman_validate.c297 struct roff_node *nc; in post_SH() local
300 nc = n->child; in post_SH()
309 if (nc != NULL && nc->type == ROFFT_TEXT && in post_SH()
310 strcmp(nc->string, tag) == 0) in post_SH()
318 if (nc != NULL) in post_SH()
325 if ((nc->tok == MAN_LP || nc->tok == MAN_PP || nc->tok == MAN_P) && in post_SH()
326 nc->body->child != NULL) { in post_SH()
327 while (nc->body->last != NULL) { in post_SH()
329 roff_node_relink(man, nc->body->last); in post_SH()
334 if (nc->tok == MAN_LP || nc->tok == MAN_PP || nc->tok == MAN_P || in post_SH()
[all …]
/freebsd/contrib/arm-optimized-routines/math/tools/
H A Dremez.jl738 nc, dc, e1 = try_e(e0)
743 return nc, dc
752 nc, dc, e2 = try_e(e1)
760 nc, dc, enew = try_e(emid)
769 return nc, dc
826 (nc, dc) = ratfn_leastsquares(f, grid, n, d, w)
828 ratfn_to_string(nc, dc))
849 approx_y = ratfn_eval(nc, dc, x)
867 return nc, dc, max_err, extrema
872 (nc, dc) = ratfn_equal_deviation(f, map(x->x[1], extrema),
[all …]
/freebsd/lib/libc/stdlib/
H A Dradixsort.c126 static int count[256], nc, bmin; in r_sort_a() local
145 if (nc == 0) { in r_sort_a()
152 nc++; in r_sort_a()
155 if (sp + nc > s + SIZE) { /* Get more stack. */ in r_sort_a()
166 if (nc == 1 && count[bmin] == n) { in r_sort_a()
168 nc = count[bmin] = 0; in r_sort_a()
187 for (cp = count + bmin; nc > 0; cp++) { in r_sort_a()
198 nc--; in r_sort_a()
225 static int count[256], nc, bmin; in r_sort_b() local
241 if (nc == 0) { in r_sort_b()
[all …]

12345678