Home
last modified time | relevance | path

Searched refs:cr2 (Results 1 – 25 of 37) sorted by relevance

12

/freebsd-head/contrib/arm-optimized-routines/math/aarch64/sve/
HDsv_sincospif_common.h52 svfloat32_t cr2 = svmul_x (pt, cr, cr); in sv_sincospif_inline() local
53 svfloat32_t cr4 = svmul_x (pt, cr2, cr2); in sv_sincospif_inline()
68 svfloat32_t cp01 = svmla_lane (sv_f32 (d->c0), cr2, c135, 0); in sv_sincospif_inline()
69 svfloat32_t cp23 = svmla_lane (sv_f32 (d->c2), cr2, c135, 1); in sv_sincospif_inline()
70 svfloat32_t cp45 = svmla_lane (sv_f32 (d->c4), cr2, c135, 2); in sv_sincospif_inline()
HDsv_sincospi_common.h59 svfloat64_t cr2 = svmul_x (pt, cr, cr); in sv_sincospi_inline() local
61 svfloat64_t cr4 = svmul_x (pt, cr2, cr2); in sv_sincospi_inline()
73 pt, sv_lw_pw_horner_9_f64_x (pg, cr2, cr4, &(d->c0), &(d->c1)), cr); in sv_sincospi_inline()
/freebsd-head/sys/security/mac_seeotheruids/
HDmac_seeotheruids.c102 seeotheruids_check(struct ucred *cr1, struct ucred *cr2) in seeotheruids_check() argument
109 if (cr1->cr_rgid == cr2->cr_rgid) in seeotheruids_check()
119 if (cr1->cr_ruid == cr2->cr_ruid) in seeotheruids_check()
153 seeotheruids_cred_check_visible(struct ucred *cr1, struct ucred *cr2) in seeotheruids_cred_check_visible() argument
156 return (seeotheruids_check(cr1, cr2)); in seeotheruids_cred_check_visible()
/freebsd-head/contrib/arm-optimized-routines/math/aarch64/advsimd/
HDv_sincospif_common.h45 float32x4_t cr2 = vmulq_f32 (cr, cr); in v_sincospif_inline() local
46 float32x4_t cr4 = vmulq_f32 (cr2, cr2); in v_sincospif_inline()
49 float32x4_t cc = vmulq_f32 (v_pw_horner_5_f32 (cr2, cr4, d->poly), cr); in v_sincospif_inline()
HDv_sincospi_common.h51 float64x2_t cr2 = vmulq_f64 (cr, cr); in v_sincospi_inline() local
52 float64x2_t cr4 = vmulq_f64 (cr2, cr2); in v_sincospi_inline()
55 float64x2_t cc = vmulq_f64 (v_pw_horner_9_f64 (cr2, cr4, d->poly), cr); in v_sincospi_inline()
/freebsd-head/sys/security/mac/
HDmac_cred.c389 mac_cred_check_visible(struct ucred *cr1, struct ucred *cr2) in mac_cred_check_visible() argument
393 MAC_POLICY_CHECK_NOSLEEP(cred_check_visible, cr1, cr2); in mac_cred_check_visible()
394 MAC_CHECK_PROBE2(cred_check_visible, error, cr1, cr2); in mac_cred_check_visible()
HDmac_framework.h134 int mac_cred_check_visible(struct ucred *cr1, struct ucred *cr2);
135 void mac_cred_copy(struct ucred *cr1, struct ucred *cr2);
/freebsd-head/tools/test/stress2/tools/
HDbench.c49 static void cr2(void);
54 static void (*functions[])(void) = {&cr1, &cr2, &cr3, &rn1, &rw1, &rw2};
92 cr2(void) in cr2() function
/freebsd-head/sys/security/mac_partition/
HDmac_partition.c135 partition_cred_check_visible(struct ucred *cr1, struct ucred *cr2) in partition_cred_check_visible() argument
139 error = partition_check(cr1->cr_label, cr2->cr_label); in partition_cred_check_visible()
/freebsd-head/sys/amd64/vmm/intel/
HDvmx_support.S64 movq %cr2,%rdi; \
81 movq %rsi,%cr2; \
/freebsd-head/sys/contrib/xen/
HDvm_event.h209 uint64_t cr2; member
361 uint64_t cr2; member
/freebsd-head/sys/amd64/amd64/
HDexception.S406 movq %cr2,%rdi /* preserve %cr2 before .. */
665 movq %cr2,%r15
704 movq %r15,%cr2
806 movq %cr2,%r15
956 movq %r15,%cr2
1014 movq %cr2,%r15
1072 movq %r15,%cr2
HDcpu_switch.S324 movq %cr2,%rax
447 movq %rax,%cr2
/freebsd-head/sys/amd64/vmm/amd/
HDvmcb.c182 *retval = state->cr2; in vmcb_read()
290 state->cr2 = val; in vmcb_write()
HDvmcb.h336 uint64_t cr2; member
/freebsd-head/stand/efi/loader/arch/amd64/
HDexc.S142 movq %cr2,%rax
/freebsd-head/sys/contrib/xen/arch-x86/hvm/
HDsave.h81 uint64_t cr2; member
195 uint64_t cr2; member
/freebsd-head/sys/contrib/xen/arch-x86/
HDxen-x86_32.h171 unsigned long cr2; member
HDxen-x86_64.h222 unsigned long cr2; member
/freebsd-head/sys/i386/i386/
HDswtch.S358 movl %cr2,%eax
412 movl %eax,%cr2
/freebsd-head/sys/contrib/xen/hvm/
HDdm_op.h336 uint64_aligned_t cr2; member
/freebsd-head/sys/contrib/alpine-hal/
HDal_hal_pcie_regs.h73 uint32_t cr2; member
/freebsd-head/usr.sbin/bhyvectl/amd64/
HDbhyvectl_machdep.c456 uint64_t cr0, cr2, cr3, cr4, dr0, dr1, dr2, dr3, dr6, dr7; in get_all_registers() local
475 error = vm_get_register(vcpu, VM_REG_GUEST_CR2, &cr2); in get_all_registers()
477 printf("cr2[%d]\t\t0x%016lx\n", vcpuid, cr2); in get_all_registers()
/freebsd-head/sys/amd64/include/
HDvmm.h784 void vm_inject_pf(struct vcpu *vcpu, int error_code, uint64_t cr2);
/freebsd-head/sys/amd64/vmm/
HDvmm.c1934 vm_inject_pf(struct vcpu *vcpu, int error_code, uint64_t cr2) in vm_inject_pf() argument
1939 error_code, cr2); in vm_inject_pf()
1941 error = vm_set_register(vcpu, VM_REG_GUEST_CR2, cr2); in vm_inject_pf()

12