| /device/linaro/bootloader/edk2/OvmfPkg/VirtioNetDxe/ |
| SnpInitialize.c | 31 @param[in,out] Dev The VNET_DEV driver instance about to enter the
49 IN OUT VNET_DEV *Dev,
60 Status = Dev->VirtIo->SetQueueSel (Dev->VirtIo, Selector);
64 Status = Dev->VirtIo->GetQueueNumMax (Dev->VirtIo, &QueueSize);
85 Status = Dev->VirtIo->SetQueueNum (Dev->VirtIo, QueueSize);
90 Status = Dev->VirtIo->SetQueueAlign (Dev->VirtIo, EFI_PAGE_SIZE);
[all...] |
| DriverBinding.c | 42 param[in,out] Dev The VNET_DEV structure being created for
59 IN OUT VNET_DEV *Dev,
76 Status = Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, NextDevStat);
82 Status = Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, NextDevStat);
88 Status = Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, NextDevStat);
96 Status = Dev->VirtIo->GetDeviceFeatures (Dev->VirtIo, &Features);
[all...] |
| Events.c | 51 VNET_DEV *Dev;
54 Dev = Context;
55 if (Dev->Snm.State != EfiSimpleNetworkInitialized) {
63 RxCurUsed = *Dev->RxRing.Used.Idx;
66 if (Dev->RxLastUsed != RxCurUsed) {
67 gBS->SignalEvent (&Dev->Snp.WaitForPacket);
85 VNET_DEV *Dev;
87 Dev = Context;
88 if (Dev->Snm.State == EfiSimpleNetworkInitialized) {
89 Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, 0);
[all...] |
| SnpGetStatus.c | 64 VNET_DEV *Dev;
74 Dev = VIRTIO_NET_FROM_SNP (This);
76 switch (Dev->Snm.State) {
90 if (Dev->Snm.MediaPresentSupported) {
93 Status = VIRTIO_CFG_READ (Dev, LinkStatus, &LinkStatus);
97 Dev->Snm.MediaPresent =
105 RxCurUsed = *Dev->RxRing.Used.Idx;
106 TxCurUsed = *Dev->TxRing.Used.Idx;
115 if (Dev->RxLastUsed != RxCurUsed) {
118 if (Dev->TxLastUsed != TxCurUsed) {
[all...] |
| SnpSharedHelpers.c | 32 @param[in,out] Dev The VNET_DEV driver instance being shut down, or whose
39 IN OUT VNET_DEV *Dev
42 FreePool (Dev->RxBuf);
49 IN OUT VNET_DEV *Dev
52 FreePool (Dev->TxFreeStack);
|
| SnpShutdown.c | 45 VNET_DEV *Dev;
53 Dev = VIRTIO_NET_FROM_SNP (This);
55 switch (Dev->Snm.State) {
66 Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, 0);
67 VirtioNetShutdownRx (Dev);
68 VirtioNetShutdownTx (Dev);
69 VirtioRingUninit (&Dev->TxRing);
70 VirtioRingUninit (&Dev->RxRing);
72 Dev->Snm.State = EfiSimpleNetworkStarted;
[all...] |
| SnpTransmit.c | 76 VNET_DEV *Dev;
86 Dev = VIRTIO_NET_FROM_SNP (This);
88 switch (Dev->Snm.State) {
99 if (BufferSize < Dev->Snm.MediaHeaderSize) {
103 if (BufferSize > Dev->Snm.MediaHeaderSize + Dev->Snm.MaxPacketSize) {
111 ASSERT (Dev->TxCurPending <= Dev->TxMaxPending);
112 if (Dev->TxCurPending == Dev->TxMaxPending) {
[all...] |
| SnpStart.c | 44 VNET_DEV *Dev;
52 Dev = VIRTIO_NET_FROM_SNP (This);
54 if (Dev->Snm.State != EfiSimpleNetworkStopped) {
58 Dev->Snm.State = EfiSimpleNetworkStarted;
|
| SnpStop.c | 45 VNET_DEV *Dev;
53 Dev = VIRTIO_NET_FROM_SNP (This);
55 if (Dev->Snm.State != EfiSimpleNetworkStarted) {
59 Dev->Snm.State = EfiSimpleNetworkStopped;
|
| SnpReceive.c | 74 VNET_DEV *Dev;
90 Dev = VIRTIO_NET_FROM_SNP (This);
92 switch (Dev->Snm.State) {
107 RxCurUsed = *Dev->RxRing.Used.Idx;
110 if (Dev->RxLastUsed == RxCurUsed) {
115 UsedElemIdx = Dev->RxLastUsed % Dev->RxRing.QueueSize;
116 DescIdx = Dev->RxRing.Used.UsedElem[UsedElemIdx].Id;
117 RxLen = Dev->RxRing.Used.UsedElem[UsedElemIdx].Len;
122 ASSERT (RxLen >= Dev->RxRing.Desc[DescIdx].Len);
[all...] |
| SnpReceiveFilters.c | 66 VNET_DEV *Dev;
74 Dev = VIRTIO_NET_FROM_SNP (This);
76 switch (Dev->Snm.State) {
98 ((Enable | Disable) & ~Dev->Snm.ReceiveFilterMask) != 0 ||
99 (!ResetMCastFilter && MCastFilterCnt > Dev->Snm.MaxMCastFilterCount)
|
| /device/linaro/bootloader/edk2/DuetPkg/FSVariable/ |
| MemStorage.c | 61 VS_DEV *Dev;
63 Status = gBS->AllocatePool (EfiRuntimeServicesData, sizeof(VS_DEV), (VOID **) &Dev);
66 ZeroMem (Dev, sizeof(VS_DEV));
68 Dev->Signature = VS_DEV_SIGNATURE;
69 Dev->Size = Size;
71 Dev->VarStore.Erase = MemEraseStore;
72 Dev->VarStore.Write = MemWriteStore;
74 Status = gBS->AllocatePool (EfiRuntimeServicesData, Size, (VOID **) &VAR_DATA_PTR (Dev));
79 *VarStore = &Dev->VarStore;
92 VS_DEV *Dev;
[all...] |
| FileStorage.c | 188 VS_DEV *Dev;
192 Dev = (VS_DEV *) Context;
194 if (VAR_FILE_DEVICEPATH (Dev) != NULL &&
195 !EFI_ERROR (CheckStoreExists (VAR_FILE_DEVICEPATH (Dev)))
214 Status = CheckStore (Handle, VAR_FILE_VOLUMEID (Dev), &Device);
220 VAR_FILE_DEVICEPATH (Dev) = Device;
222 VAR_FILE_DEVICEPATH (Dev),
223 VAR_FILE_FILEPATH (Dev),
229 NumBytes = Dev->Size;
230 Status = File->Write (File, &NumBytes, VAR_DATA_PTR (Dev));
[all...] |
| /device/linaro/bootloader/edk2/OvmfPkg/VirtioPciDeviceDxe/ |
| VirtioPciFunctions.c | 57 VIRTIO_PCI_DEVICE *Dev;
59 Dev = VIRTIO_PCI_DEVICE_FROM_VIRTIO_DEVICE (This);
61 return VirtioPciIoRead (Dev,
62 Dev->DeviceSpecificConfigurationOffset + FieldOffset,
92 VIRTIO_PCI_DEVICE *Dev;
94 Dev = VIRTIO_PCI_DEVICE_FROM_VIRTIO_DEVICE (This);
96 return VirtioPciIoWrite (Dev,
97 Dev->DeviceSpecificConfigurationOffset + FieldOffset, FieldSize, Value);
107 VIRTIO_PCI_DEVICE *Dev;
115 Dev = VIRTIO_PCI_DEVICE_FROM_VIRTIO_DEVICE (This);
[all...] |
| /external/eigen/unsupported/Eigen/CXX11/src/Tensor/ |
| TensorSyclExtractFunctors.h | 47 template <template <class, class> class UnaryCategory, typename OP, typename RHSExpr, typename Dev>
48 struct FunctorExtractor<TensorEvaluator<const UnaryCategory<OP, RHSExpr>, Dev> > {
49 FunctorExtractor<TensorEvaluator<RHSExpr, Dev> > rhsExpr;
51 FunctorExtractor(const TensorEvaluator<const UnaryCategory<OP, RHSExpr>, Dev>& expr)
56 template <template <class, class> class UnaryCategory, typename OP, typename RHSExpr, typename Dev>
57 struct FunctorExtractor<TensorEvaluator<UnaryCategory<OP, RHSExpr>, Dev> >
58 : FunctorExtractor<TensorEvaluator<const UnaryCategory<OP, RHSExpr>, Dev> >{};
62 template <template<class, class, class> class BinaryCategory, typename OP, typename LHSExpr, typename RHSExpr, typename Dev>
63 struct FunctorExtractor<TensorEvaluator<const BinaryCategory<OP, LHSExpr, RHSExpr>, Dev> > {
64 FunctorExtractor<TensorEvaluator<LHSExpr, Dev> > lhsExpr
[all...] |
| TensorSyclExtractAccessor.h | 68 template <template<class, class> class UnaryCategory, typename OP, typename RHSExpr, typename Dev>
69 struct ExtractAccessor<TensorEvaluator<const UnaryCategory<OP, RHSExpr>, Dev> > {
70 static inline auto getTuple(cl::sycl::handler& cgh, const TensorEvaluator<const UnaryCategory<OP, RHSExpr>, Dev> eval)
77 template <template<class, class> class UnaryCategory, typename OP, typename RHSExpr, typename Dev>
78 struct ExtractAccessor<TensorEvaluator<UnaryCategory<OP, RHSExpr>, Dev> >
79 : ExtractAccessor<TensorEvaluator<const UnaryCategory<OP, RHSExpr>, Dev> > {};
82 template <template<class, class, class> class BinaryCategory, typename OP, typename LHSExpr, typename RHSExpr, typename Dev>
83 struct ExtractAccessor<TensorEvaluator<const BinaryCategory<OP, LHSExpr, RHSExpr>, Dev> > {
84 static inline auto getTuple(cl::sycl::handler& cgh, const TensorEvaluator<const BinaryCategory<OP, LHSExpr, RHSExpr>, Dev> eval)
90 template <template<class, class, class> class BinaryCategory, typename OP, typename LHSExpr, typename RHSExpr, typename Dev>
[all...] |
| /device/linaro/bootloader/edk2/OvmfPkg/VirtioBlkDxe/ |
| VirtioBlk.c | 45 @param[in] Dev Pointer to the VBLK_DEV structure whose VirtIo space
46 we're accessing. Dev->VirtIo must be valid.
64 #define VIRTIO_CFG_WRITE(Dev, Field, Value) ((Dev)->VirtIo->WriteDevice ( \
65 (Dev)->VirtIo, \
71 #define VIRTIO_CFG_READ(Dev, Field, Pointer) ((Dev)->VirtIo->ReadDevice ( \
72 (Dev)->VirtIo, \
197 @param[in] Dev The virtio-blk device the request is targeted
242 IN VBLK_DEV *Dev,
[all...] |
| /device/linaro/bootloader/edk2/OvmfPkg/XenPvBlkDxe/ |
| BlockFront.c | 82 @param Dev The instance to free.
87 IN XEN_BLOCK_FRONT_DEVICE *Dev
90 XENBUS_PROTOCOL *XenBusIo = Dev->XenBusIo;
92 if (Dev->RingRef != 0) {
93 XenBusIo->GrantEndAccess (XenBusIo, Dev->RingRef);
95 if (Dev->Ring.sring != NULL) {
96 FreePages (Dev->Ring.sring, 1);
98 if (Dev->EventChannel != 0) {
99 XenBusIo->EventChannelClose (XenBusIo, Dev->EventChannel);
101 FreePool (Dev);
[all...] |
| /device/linaro/bootloader/edk2/OvmfPkg/VirtioRngDxe/ |
| VirtioRng.c | 135 VIRTIO_RNG_DEV *Dev;
160 Dev = VIRTIO_ENTROPY_SOURCE_FROM_RNG (This);
170 VirtioPrepare (&Dev->Ring, &Indices);
171 VirtioAppendDesc (&Dev->Ring,
177 if (VirtioFlush (Dev->VirtIo, 0, &Dev->Ring, &Indices, &Len) !=
200 IN OUT VIRTIO_RNG_DEV *Dev
212 Status = Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, NextDevStat);
218 Status = Dev->VirtIo->SetDeviceStatus (Dev->VirtIo, NextDevStat);
[all...] |
| /device/linaro/bootloader/edk2/OvmfPkg/VirtioScsiDxe/ |
| VirtioScsi.c | 60 @param[in] Dev Pointer to the VSCSI_DEV structure.
77 #define VIRTIO_CFG_WRITE(Dev, Field, Value) ((Dev)->VirtIo->WriteDevice ( \
78 (Dev)->VirtIo, \
84 #define VIRTIO_CFG_READ(Dev, Field, Pointer) ((Dev)->VirtIo->ReadDevice ( \
85 (Dev)->VirtIo, \
123 @param[in] Dev The virtio-scsi host device the packet targets.
154 IN CONST VSCSI_DEV *Dev,
168 !Dev->InOutSupported) ||
[all...] |
| /device/linaro/bootloader/edk2/OvmfPkg/XenBusDxe/ |
| XenBusDxe.c | 57 @param Dev A XENBUS_DEVICE instance.
59 @retval EFI_SUCCESS Dev->SharedInfo whill contain a pointer to
67 IN OUT XENBUS_DEVICE *Dev
72 ASSERT (Dev->SharedInfo == NULL);
83 Dev->SharedInfo = AllocateReservedPages (1);
84 Parameter.gpfn = (UINTN) Dev->SharedInfo >> EFI_PAGE_SHIFT;
86 FreePages (Dev->SharedInfo, 1);
87 Dev->SharedInfo = NULL;
267 XENBUS_DEVICE *Dev = Context;
269 gBS->DisconnectController(Dev->ControllerHandle,
[all...] |
| /device/linaro/bootloader/edk2/SecurityPkg/Tcg/Opal/OpalPasswordDxe/ |
| OpalHiiCallbacks.c | 36 OPAL_DRIVER_DEVICE* Dev;
42 Dev = DRIVER_DEVICE_FROM_OPALDISK(OpalDisk);
43 if (Dev == NULL) {
50 if (Dev->Name16 != NULL) {
51 NameLen = StrLen(Dev->Name16);
62 if (Dev->Name16 != NULL) {
63 CopyMem(VarName + PrefixLen, Dev->Name16, NameLen * sizeof(CHAR16));
134 OPAL_DRIVER_DEVICE* Dev;
137 Dev = OpalDriverGetDeviceList();
144 while (Dev != NULL) {
[all...] |
| OpalDriver.c | 46 @param Dev New create device.
51 IN OPAL_DRIVER_DEVICE *Dev
57 mOpalDriver.DeviceList = Dev;
64 TmpDev->Next = Dev;
71 @param Dev The device need to be removed.
76 IN OPAL_DRIVER_DEVICE *Dev
85 if (mOpalDriver.DeviceList == Dev) {
92 if (TmpDev->Next == Dev) {
93 TmpDev->Next = Dev->Next;
127 @param[in] Dev The device which need to be unlock.
[all...] |
| /device/linaro/bootloader/OpenPlatformPkg/Chips/Hisilicon/Library/DS3231RealTimeClockLib/ |
| DS3231RealTimeClockLib.c | 63 I2C_DEVICE Dev;
70 (VOID) CopyMem(&Dev, &gDS3231RtcDevice, sizeof(Dev));
72 Status = I2CInit(Dev.Socket,Dev.Port,Normal);
77 Status = I2CRead(&Dev,DS3231_REGADDR_CONTROL,1,&Temp.u8);
82 Status = I2CWrite(&Dev,DS3231_REGADDR_CONTROL,1,&Temp.u8);
88 Status = I2CRead(&Dev,DS3231_REGADDR_HOURS,1,&Hours.u8);
93 Status = I2CWrite(&Dev,DS3231_REGADDR_HOURS,1,&Hours.u8);
131 I2C_DEVICE Dev;
[all...] |
| /device/linaro/bootloader/edk2/MdeModulePkg/Bus/Pci/NonDiscoverablePciDeviceDxe/ |
| NonDiscoverablePciDeviceIo.c | 34 @param Dev Point to the NON_DISCOVERABLE_PCI_DEVICE instance.
42 IN NON_DISCOVERABLE_PCI_DEVICE *Dev,
49 if (BarIndex < Dev->BarOffset) {
53 BarIndex -= (UINT8)Dev->BarOffset;
55 for (Desc = Dev->Device->Resources;
234 NON_DISCOVERABLE_PCI_DEVICE *Dev;
244 Dev = NON_DISCOVERABLE_PCI_DEVICE_FROM_PCI_IO(This);
249 Status = GetBarResource (Dev, BarIndex, &Desc);
321 NON_DISCOVERABLE_PCI_DEVICE *Dev;
331 Dev = NON_DISCOVERABLE_PCI_DEVICE_FROM_PCI_IO(This);
[all...] |
