unsafe {
    let surface = surface.as_hal::<wgpu::hal::metal::Api>();
    if let Some(surface_ref) = surface {
        let surface_ptr: *const wgpu::hal::metal::Surface = &*surface_ref;
        let surface_mut_ptr: *mut wgpu::hal::metal::Surface = surface_ptr as *mut _;
        #[allow(invalid_reference_casting)]
        let surface_mut = &mut *surface_mut_ptr;
        surface_mut.present_with_transaction = true;
    }
}

let config = wgpu::SurfaceConfiguration {
    usage: wgpu::TextureUsages::RENDER_ATTACHMENT,
    format: surface_format,
    width: size.width,
    height: size.height,
    present_mode: wgpu::PresentMode::Fifo,
    alpha_mode: surface_caps.alpha_modes[0],
    view_formats: vec![],
    desired_maximum_frame_latency: 2,
};