// Copyright 2017 The Dawn Authors // // Licensed under the Apache License, Version 2.0 (the "License"); // you may not use this file except in compliance with the License. // You may obtain a copy of the License at // // http://www.apache.org/licenses/LICENSE-2.0 // // Unless required by applicable law or agreed to in writing, software // distributed under the License is distributed on an "AS IS" BASIS, // WITHOUT WARRANTIES OR CONDITIONS OF ANY KIND, either express or implied. // See the License for the specific language governing permissions and // limitations under the License. #include "dawn_native/metal/SwapChainMTL.h" #include "dawn_native/Surface.h" #include "dawn_native/metal/DeviceMTL.h" #include "dawn_native/metal/TextureMTL.h" #include #import namespace dawn_native { namespace metal { // OldSwapChain OldSwapChain::OldSwapChain(Device* device, const SwapChainDescriptor* descriptor) : OldSwapChainBase(device, descriptor) { const auto& im = GetImplementation(); DawnWSIContextMetal wsiContext = {}; wsiContext.device = ToBackend(GetDevice())->GetMTLDevice(); wsiContext.queue = ToBackend(GetDevice())->GetMTLQueue(); im.Init(im.userData, &wsiContext); } OldSwapChain::~OldSwapChain() { } TextureBase* OldSwapChain::GetNextTextureImpl(const TextureDescriptor* descriptor) { const auto& im = GetImplementation(); DawnSwapChainNextTexture next = {}; DawnSwapChainError error = im.GetNextTexture(im.userData, &next); if (error) { GetDevice()->HandleError(InternalErrorType::Internal, error); return nullptr; } id nativeTexture = reinterpret_cast>(next.texture.ptr); return new Texture(ToBackend(GetDevice()), descriptor, nativeTexture); } MaybeError OldSwapChain::OnBeforePresent(TextureViewBase*) { return {}; } // SwapChain // static ResultOrError SwapChain::Create(Device* device, Surface* surface, NewSwapChainBase* previousSwapChain, const SwapChainDescriptor* descriptor) { std::unique_ptr swapchain = std::make_unique(device, surface, descriptor); DAWN_TRY(swapchain->Initialize(previousSwapChain)); return swapchain.release(); } SwapChain::~SwapChain() { DetachFromSurface(); } MaybeError SwapChain::Initialize(NewSwapChainBase* previousSwapChain) { ASSERT(GetSurface()->GetType() == Surface::Type::MetalLayer); if (previousSwapChain != nullptr) { // TODO(cwallez@chromium.org): figure out what should happen when surfaces are used by // multiple backends one after the other. It probably needs to block until the backend // and GPU are completely finished with the previous swapchain. if (previousSwapChain->GetBackendType() != wgpu::BackendType::Metal) { return DAWN_VALIDATION_ERROR("metal::SwapChain cannot switch between APIs"); } previousSwapChain->DetachFromSurface(); } mLayer = static_cast(GetSurface()->GetMetalLayer()); ASSERT(mLayer != nullptr); CGSize size = {}; size.width = GetWidth(); size.height = GetHeight(); [*mLayer setDrawableSize:size]; [*mLayer setFramebufferOnly:(GetUsage() == wgpu::TextureUsage::RenderAttachment)]; [*mLayer setDevice:ToBackend(GetDevice())->GetMTLDevice()]; [*mLayer setPixelFormat:MetalPixelFormat(GetFormat())]; #if defined(DAWN_PLATFORM_MACOS) if (@available(macos 10.13, *)) { [*mLayer setDisplaySyncEnabled:(GetPresentMode() != wgpu::PresentMode::Immediate)]; } #endif // defined(DAWN_PLATFORM_MACOS) // There is no way to control Fifo vs. Mailbox in Metal. return {}; } MaybeError SwapChain::PresentImpl() { ASSERT(mCurrentDrawable != nullptr); [*mCurrentDrawable present]; mTexture->Destroy(); mTexture = nullptr; mCurrentDrawable = nullptr; return {}; } ResultOrError SwapChain::GetCurrentTextureViewImpl() { ASSERT(mCurrentDrawable == nullptr); mCurrentDrawable = [*mLayer nextDrawable]; TextureDescriptor textureDesc = GetSwapChainBaseTextureDescriptor(this); mTexture = AcquireRef( new Texture(ToBackend(GetDevice()), &textureDesc, [*mCurrentDrawable texture])); return mTexture->CreateView(); } void SwapChain::DetachFromSurfaceImpl() { ASSERT((mTexture == nullptr) == (mCurrentDrawable == nullptr)); if (mTexture != nullptr) { mTexture->Destroy(); mTexture = nullptr; mCurrentDrawable = nullptr; } } }} // namespace dawn_native::metal