/freebsd/contrib/llvm-project/clang/include/clang/Basic/ |
H A D | BuiltinsMips.def | 29 BUILTIN(__builtin_mips_madd, "LLiLLiii", "nc") 31 BUILTIN(__builtin_mips_msub, "LLiLLiii", "nc") 40 BUILTIN(__builtin_mips_modsub, "iii", "nc") 69 BUILTIN(__builtin_mips_shra_r_w, "iii", "nc") 82 BUILTIN(__builtin_mips_mult, "LLiii", "nc") 114 BUILTIN(__builtin_mips_bitrev, "ii", "nc") 132 BUILTIN(__builtin_mips_addqh_w, "iii", "nc") 302 BUILTIN(__builtin_msa_bnz_h, "iV8Us", "nc") 303 BUILTIN(__builtin_msa_bnz_w, "iV4Ui", "nc") 323 BUILTIN(__builtin_msa_bz_h, "iV8Us", "nc") [all …]
|
H A D | BuiltinsLoongArchLASX.def | 15 TARGET_BUILTIN(__builtin_lasx_xvadd_b, "V32cV32cV32c", "nc", "lasx") 16 TARGET_BUILTIN(__builtin_lasx_xvadd_h, "V16sV16sV16s", "nc", "lasx") 17 TARGET_BUILTIN(__builtin_lasx_xvadd_w, "V8iV8iV8i", "nc", "lasx") 21 TARGET_BUILTIN(__builtin_lasx_xvsub_b, "V32cV32cV32c", "nc", "lasx") 22 TARGET_BUILTIN(__builtin_lasx_xvsub_h, "V16sV16sV16s", "nc", "lasx") 23 TARGET_BUILTIN(__builtin_lasx_xvsub_w, "V8iV8iV8i", "nc", "lasx") 29 TARGET_BUILTIN(__builtin_lasx_xvaddi_wu, "V8iV8iIUi", "nc", "lasx") 37 TARGET_BUILTIN(__builtin_lasx_xvneg_b, "V32cV32c", "nc", "lasx") 38 TARGET_BUILTIN(__builtin_lasx_xvneg_h, "V16sV16s", "nc", "lasx") 39 TARGET_BUILTIN(__builtin_lasx_xvneg_w, "V8iV8i", "nc", "lasx") [all …]
|
H A D | BuiltinsLoongArchLSX.def | 15 TARGET_BUILTIN(__builtin_lsx_vadd_b, "V16cV16cV16c", "nc", "lsx") 16 TARGET_BUILTIN(__builtin_lsx_vadd_h, "V8sV8sV8s", "nc", "lsx") 17 TARGET_BUILTIN(__builtin_lsx_vadd_w, "V4iV4iV4i", "nc", "lsx") 21 TARGET_BUILTIN(__builtin_lsx_vsub_b, "V16cV16cV16c", "nc", "lsx") 22 TARGET_BUILTIN(__builtin_lsx_vsub_h, "V8sV8sV8s", "nc", "lsx") 23 TARGET_BUILTIN(__builtin_lsx_vsub_w, "V4iV4iV4i", "nc", "lsx") 37 TARGET_BUILTIN(__builtin_lsx_vneg_b, "V16cV16c", "nc", "lsx") 38 TARGET_BUILTIN(__builtin_lsx_vneg_h, "V8sV8s", "nc", "lsx") 39 TARGET_BUILTIN(__builtin_lsx_vneg_w, "V4iV4i", "nc", "lsx") 952 TARGET_BUILTIN(__builtin_lsx_bz_h, "iV8Us", "nc", "lsx") [all …]
|
H A D | BuiltinsSystemZ.def | 35 TARGET_BUILTIN(__builtin_s390_lcbb, "UivC*Ii", "nc", "vector") 53 TARGET_BUILTIN(__builtin_s390_vuphb, "V8SsV16Sc", "nc", "vector") 54 TARGET_BUILTIN(__builtin_s390_vuphh, "V4SiV8Ss", "nc", "vector") 56 TARGET_BUILTIN(__builtin_s390_vuplb, "V8SsV16Sc", "nc", "vector") 57 TARGET_BUILTIN(__builtin_s390_vuplhw, "V4SiV8Ss", "nc", "vector") 60 TARGET_BUILTIN(__builtin_s390_vuplhh, "V4UiV8Us", "nc", "vector") 63 TARGET_BUILTIN(__builtin_s390_vupllh, "V4UiV8Us", "nc", "vector") 97 TARGET_BUILTIN(__builtin_s390_vclzh, "V8UsV8Us", "nc", "vector") 98 TARGET_BUILTIN(__builtin_s390_vclzf, "V4UiV4Ui", "nc", "vector") 101 TARGET_BUILTIN(__builtin_s390_vctzh, "V8UsV8Us", "nc", "vector") [all …]
|
H A D | BuiltinsAMDGPU.def | 88 BUILTIN(__builtin_amdgcn_rcp, "dd", "nc") 89 BUILTIN(__builtin_amdgcn_rcpf, "ff", "nc") 90 BUILTIN(__builtin_amdgcn_sqrt, "dd", "nc") 91 BUILTIN(__builtin_amdgcn_sqrtf, "ff", "nc") 92 BUILTIN(__builtin_amdgcn_rsq, "dd", "nc") 93 BUILTIN(__builtin_amdgcn_rsqf, "ff", "nc") 96 BUILTIN(__builtin_amdgcn_sinf, "ff", "nc") 97 BUILTIN(__builtin_amdgcn_cosf, "ff", "nc") 98 BUILTIN(__builtin_amdgcn_logf, "ff", "nc") 99 BUILTIN(__builtin_amdgcn_exp2f, "ff", "nc") [all …]
|
H A D | BuiltinsWebAssembly.def | 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") 53 BUILTIN(__builtin_wasm_trunc_s_i64_f32, "LLif", "nc") 54 BUILTIN(__builtin_wasm_trunc_u_i64_f32, "LLif", "nc") [all …]
|
H A D | BuiltinsLoongArchBase.def | 16 TARGET_BUILTIN(__builtin_loongarch_cacop_w, "viUii", "nc", "32bit") 17 TARGET_BUILTIN(__builtin_loongarch_dbar, "vIUi", "nc", "") 18 TARGET_BUILTIN(__builtin_loongarch_ibar, "vIUi", "nc", "") 19 TARGET_BUILTIN(__builtin_loongarch_movfcsr2gr, "UiIUi", "nc", "f") 21 TARGET_BUILTIN(__builtin_loongarch_break, "vIUi", "nc", "") 22 TARGET_BUILTIN(__builtin_loongarch_syscall, "vIUi", "nc", "") 23 TARGET_BUILTIN(__builtin_loongarch_cpucfg, "UiUi", "nc", "") 36 TARGET_BUILTIN(__builtin_loongarch_csrrd_w, "UiIUi", "nc", "") 43 TARGET_BUILTIN(__builtin_loongarch_iocsrrd_b, "UiUi", "nc", "") 44 TARGET_BUILTIN(__builtin_loongarch_iocsrrd_h, "UiUi", "nc", "") [all …]
|
H A D | BuiltinsRISCV.def | 19 TARGET_BUILTIN(__builtin_riscv_orc_b_32, "UiUi", "nc", "zbb") 21 TARGET_BUILTIN(__builtin_riscv_clz_32, "UiUi", "nc", "zbb|xtheadbb") 23 TARGET_BUILTIN(__builtin_riscv_ctz_32, "UiUi", "nc", "zbb") 24 TARGET_BUILTIN(__builtin_riscv_ctz_64, "UiUWi", "nc", "zbb,64bit") 41 TARGET_BUILTIN(__builtin_riscv_brev8_32, "UiUi", "nc", "zbkb") 64 TARGET_BUILTIN(__builtin_riscv_sha256sig0, "UiUi", "nc", "zknh") 65 TARGET_BUILTIN(__builtin_riscv_sha256sig1, "UiUi", "nc", "zknh") 66 TARGET_BUILTIN(__builtin_riscv_sha256sum0, "UiUi", "nc", "zknh") 67 TARGET_BUILTIN(__builtin_riscv_sha256sum1, "UiUi", "nc", "zknh") 85 TARGET_BUILTIN(__builtin_riscv_sm3p0, "UiUi", "nc", "zksh") [all …]
|
H A D | BuiltinsARM.def | 32 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") 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") 61 BUILTIN(__builtin_arm_sel, "iii", "nc") 82 BUILTIN(__builtin_arm_qasx, "iii", "nc") [all …]
|
/freebsd/sys/dev/ntb/ |
H A D | ntb.c | 100 nc = malloc(sizeof(*nc), M_DEVBUF, M_WAITOK | M_ZERO); in ntb_register_device() 115 device_set_ivars(nc->dev, nc); in ntb_register_device() 116 *cpp = nc; in ntb_register_device() 186 printf("-%d", nc->mwoff + nc->mwcnt - 1); in ntb_print_child() 191 printf("-%d", nc->spadoff + nc->spadcnt - 1); in ntb_print_child() 196 printf("-%d", nc->dboff + nc->dbcnt - 1); in ntb_print_child() 227 for (nc = *cpp; nc != NULL; nc = nc->next) { in ntb_link_event() 230 nc->ctx_ops->link_event(nc->ctx); in ntb_link_event() 242 for (nc = *cpp; nc != NULL; nc = nc->next) { in ntb_db_event() 245 nc->ctx_ops->db_event(nc->ctx, vec); in ntb_db_event() [all …]
|
/freebsd/lib/libnvmf/ |
H A D | nvmf_transport.c | 130 if (nc == NULL) in nvmf_allocate_command() 133 nc->nc_qpair = qp; in nvmf_allocate_command() 135 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command() 140 return (nc); in nvmf_allocate_command() 149 if (nc == NULL) in nvmf_allocate_response() 152 nc->nc_qpair = qp; in nvmf_allocate_response() 154 memcpy(&nc->nc_cqe, cqe, nc->nc_qe_len); in nvmf_allocate_response() 155 return (nc); in nvmf_allocate_response() 167 nc->nc_data = buf; in nvmf_capsule_append_data() 176 nc->nc_qpair->nq_association->na_ops->free_capsule(nc); in nvmf_free_capsule() [all …]
|
H A D | nvmf_tcp.c | 80 #define TCAP(nc) ((struct nvmf_tcp_capsule *)(nc)) argument 81 #define CTCAP(nc) ((const struct nvmf_tcp_capsule *)(nc)) argument 377 if (nc == NULL) in nvmf_tcp_save_command_capsule() 380 tc = TCAP(nc); in nvmf_tcp_save_command_capsule() 398 if (nc == NULL) in nvmf_tcp_save_response_capsule() 402 tc = TCAP(nc); in nvmf_tcp_save_response_capsule() 1147 nc = calloc(1, sizeof(*nc)); in tcp_allocate_capsule() 1148 return (&nc->nc); in tcp_allocate_capsule() 1173 if (nc->nc_data_len != 0 && nc->nc_send_data && in tcp_transmit_command() 1196 nc->nc_data : NULL, use_icd ? nc->nc_data_len : 0); in tcp_transmit_command() [all …]
|
H A D | libnvmf.h | 102 void nvmf_free_capsule(struct nvmf_capsule *nc); 103 int nvmf_capsule_append_data(struct nvmf_capsule *nc, 105 int nvmf_transmit_capsule(struct nvmf_capsule *nc); 107 const void *nvmf_capsule_sqe(const struct nvmf_capsule *nc); 108 const void *nvmf_capsule_cqe(const struct nvmf_capsule *nc); 139 int nvmf_receive_controller_data(const struct nvmf_capsule *nc, 149 int nvmf_send_controller_data(const struct nvmf_capsule *nc, 157 void nvmf_init_cqe(void *cqe, const struct nvmf_capsule *nc, 184 int nvmf_send_generic_error(const struct nvmf_capsule *nc, 188 int nvmf_send_success(const struct nvmf_capsule *nc); [all …]
|
H A D | nvmf_controller.c | 38 nvmf_init_cqe(&cpl, nc, status); 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() 62 *ncp = nc; in nvmf_controller_receive_capsule() 69 struct nvmf_qpair *qp = nc->nc_qpair; in nvmf_controller_transmit_response() 74 nc->nc_cqe.sqhd = htole16(qp->nq_sqhd); in nvmf_controller_transmit_response() 76 nc->nc_cqe.sqhd = 0; in nvmf_controller_transmit_response() [all …]
|
/freebsd/sys/dev/nvmf/ |
H A D | nvmf_transport.c | 102 if (nc == NULL) in nvmf_allocate_command() 105 nc->nc_qpair = qp; in nvmf_allocate_command() 107 memcpy(&nc->nc_sqe, sqe, nc->nc_qe_len); in nvmf_allocate_command() 112 return (nc); in nvmf_allocate_command() 123 if (nc == NULL) in nvmf_allocate_response() 128 memcpy(&nc->nc_cqe, cqe, nc->nc_qe_len); in nvmf_allocate_response() 129 return (nc); in nvmf_allocate_response() 151 nc->nc_qpair->nq_ops->free_capsule(nc); in nvmf_free_capsule() 157 return (nc->nc_qpair->nq_ops->transmit_capsule(nc)); in nvmf_transmit_capsule() 192 return (nc->nc_qpair->nq_ops->validate_command_capsule(nc)); in nvmf_validate_command_capsule() [all …]
|
H A D | nvmf_transport.h | 73 void nvmf_free_capsule(struct nvmf_capsule *nc); 74 int nvmf_capsule_append_data(struct nvmf_capsule *nc, 77 int nvmf_transmit_capsule(struct nvmf_capsule *nc); 78 void nvmf_abort_capsule_data(struct nvmf_capsule *nc, int error); 79 void *nvmf_capsule_sqe(struct nvmf_capsule *nc); 80 void *nvmf_capsule_cqe(struct nvmf_capsule *nc); 90 uint8_t nvmf_validate_command_capsule(struct nvmf_capsule *nc); 108 int nvmf_receive_controller_data(struct nvmf_capsule *nc, 134 u_int nvmf_send_controller_data(struct nvmf_capsule *nc,
|
H A D | nvmf_transport_internal.h | 30 void (*free_capsule)(struct nvmf_capsule *nc); 31 int (*transmit_capsule)(struct nvmf_capsule *nc); 32 uint8_t (*validate_command_capsule)(struct nvmf_capsule *nc); 35 size_t (*capsule_data_len)(const struct nvmf_capsule *nc); 36 int (*receive_controller_data)(struct nvmf_capsule *nc, 38 u_int (*send_controller_data)(struct nvmf_capsule *nc, 105 nvmf_capsule_received(struct nvmf_qpair *nq, struct nvmf_capsule *nc) in nvmf_capsule_received() argument 107 nq->nq_receive(nq->nq_receive_arg, nc); in nvmf_capsule_received()
|
/freebsd/usr.sbin/nvmfd/ |
H A D | io.c | 242 nvmf_send_success(nc); in handle_set_features() 273 nvmf_send_success(nc); in admin_command() 325 nvmf_send_success(nc); in handle_io_fabrics_command() 445 nvmf_free_capsule(nc); in handle_io_commands() 517 nvmf_free_capsule(nc); in connect_admin_qpair() 524 nvmf_free_capsule(nc); in connect_admin_qpair() 600 nvmf_free_capsule(nc); in connect_io_qpair() 606 nvmf_free_capsule(nc); in connect_io_qpair() 626 nc = NULL; in io_socket_thread() 657 if (nc != NULL) in io_socket_thread() [all …]
|
H A D | controller.c | 66 nvmf_init_cqe(&rsp, nc, 0); in handle_property_get() 93 nvmf_send_response(nc, &rsp); in handle_property_get() 114 nvmf_send_success(nc); in handle_property_set() 126 handle_property_get(c, nc, in handle_fabrics_command() 130 handle_property_set(c, nc, in handle_fabrics_command() 176 struct nvmf_capsule *nc; in controller_handle_admin_commands() local 187 cmd = nvmf_capsule_sqe(nc); in controller_handle_admin_commands() 199 nvmf_free_capsule(nc); in controller_handle_admin_commands() 203 if (cb(nc, cmd, cb_arg)) { in controller_handle_admin_commands() 204 nvmf_free_capsule(nc); in controller_handle_admin_commands() [all …]
|
H A D | devices.c | 235 const struct nvmf_capsule *nc) in device_read() argument 244 nvmf_send_generic_error(nc, in device_read() 256 if (nvmf_capsule_data_len(nc) != len) { in device_read() 268 nvmf_send_generic_error(nc, in device_read() 301 const struct nvmf_capsule *nc) in device_write() argument 311 nvmf_send_generic_error(nc, in device_write() 323 if (nvmf_capsule_data_len(nc) != len) { in device_write() 346 nvmf_send_generic_error(nc, in device_write() 352 nvmf_send_success(nc); in device_write() 362 nvmf_send_generic_error(nc, in device_flush() [all …]
|
/freebsd/tools/diag/dumpvfscache/ |
H A D | dumpvfscache.c | 72 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/sbin/bsdlabel/ |
H A D | disktab | 25 :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:\ 175 :ns#2880:nc#1:\ 180 :ns#5760:nc#1:\ 185 :ns#8640:nc#1:\ [all …]
|
/freebsd/sys/dev/nvmf/controller/ |
H A D | nvmft_controller.c | 631 nvmf_free_capsule(nc); in handle_get_log_page() 657 nvmf_free_capsule(nc); in handle_identify_command() 706 nvmf_free_capsule(nc); in handle_identify_command() 756 nvmf_free_capsule(nc); in handle_set_features() 783 nvmf_free_capsule(nc); in handle_set_features() 934 nvmf_free_capsule(nc); in handle_admin_fabrics_command() 950 nvmf_free_capsule(nc); in nvmft_handle_admin_command() 980 nvmf_free_capsule(nc); in nvmft_handle_admin_command() 984 nvmf_free_capsule(nc); in nvmft_handle_admin_command() 994 nvmf_free_capsule(nc); in nvmft_handle_admin_command() [all …]
|
H A D | nvmft_qpair.c | 43 struct nvmf_capsule *nc, uint8_t sc_status); 72 cmd = nvmf_capsule_sqe(nc); in nvmft_receive_capsule() 76 nvmf_free_capsule(nc); in nvmft_receive_capsule() 80 sc_status = nvmf_validate_command_capsule(nc); in nvmft_receive_capsule() 82 _nvmft_send_generic_error(qp, nc, sc_status); in nvmft_receive_capsule() 83 nvmf_free_capsule(nc); in nvmft_receive_capsule() 90 nvmf_free_capsule(nc); in nvmft_receive_capsule() 95 nvmft_handle_admin_command(ctrlr, nc); in nvmft_receive_capsule() 97 nvmft_handle_io_command(qp, qp->qid, nc); in nvmft_receive_capsule() 250 nvmft_init_cqe(&cpl, nc, status); in nvmft_send_error() [all …]
|
/freebsd/tests/sys/netpfil/pf/ |
H A D | sctp.sh | 65 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) 139 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 & 155 echo "foo" | jexec ${j}a nc -6 --sctp -N -l 1234 & 212 echo "foo" | jexec ${j}a nc --sctp -N -l 1234 & 436 echo "foo" | jexec ${j}c nc --sctp -N -l 1234 & [all …]
|