1use crate::{
2 executor,
3 geometry::{
4 rect::RectF,
5 vector::{vec2f, Vector2F},
6 },
7 keymap::Keystroke,
8 platform::{self, Event, WindowBounds, WindowContext},
9 Scene,
10};
11use block::ConcreteBlock;
12use cocoa::{
13 appkit::{
14 CGPoint, NSApplication, NSBackingStoreBuffered, NSScreen, NSView, NSViewHeightSizable,
15 NSViewWidthSizable, NSWindow, NSWindowButton, NSWindowStyleMask,
16 },
17 base::{id, nil},
18 foundation::{NSAutoreleasePool, NSInteger, NSSize, NSString},
19 quartzcore::AutoresizingMask,
20};
21use core_graphics::display::CGRect;
22use ctor::ctor;
23use foreign_types::ForeignType as _;
24use objc::{
25 class,
26 declare::ClassDecl,
27 msg_send,
28 runtime::{Class, Object, Protocol, Sel, BOOL, NO, YES},
29 sel, sel_impl,
30};
31use postage::oneshot;
32use smol::Timer;
33use std::{
34 any::Any,
35 cell::{Cell, RefCell},
36 convert::TryInto,
37 ffi::c_void,
38 mem, ptr,
39 rc::{Rc, Weak},
40 sync::Arc,
41 time::Duration,
42};
43
44use super::{geometry::RectFExt, renderer::Renderer};
45
46const WINDOW_STATE_IVAR: &'static str = "windowState";
47
48static mut WINDOW_CLASS: *const Class = ptr::null();
49static mut VIEW_CLASS: *const Class = ptr::null();
50
51#[allow(non_upper_case_globals)]
52const NSViewLayerContentsRedrawDuringViewResize: NSInteger = 2;
53
54#[ctor]
55unsafe fn build_classes() {
56 WINDOW_CLASS = {
57 let mut decl = ClassDecl::new("GPUIWindow", class!(NSWindow)).unwrap();
58 decl.add_ivar::<*mut c_void>(WINDOW_STATE_IVAR);
59 decl.add_method(sel!(dealloc), dealloc_window as extern "C" fn(&Object, Sel));
60 decl.add_method(
61 sel!(canBecomeMainWindow),
62 yes as extern "C" fn(&Object, Sel) -> BOOL,
63 );
64 decl.add_method(
65 sel!(canBecomeKeyWindow),
66 yes as extern "C" fn(&Object, Sel) -> BOOL,
67 );
68 decl.add_method(
69 sel!(sendEvent:),
70 send_event as extern "C" fn(&Object, Sel, id),
71 );
72 decl.add_method(
73 sel!(windowDidResize:),
74 window_did_resize as extern "C" fn(&Object, Sel, id),
75 );
76 decl.add_method(sel!(close), close_window as extern "C" fn(&Object, Sel));
77 decl.register()
78 };
79
80 VIEW_CLASS = {
81 let mut decl = ClassDecl::new("GPUIView", class!(NSView)).unwrap();
82 decl.add_ivar::<*mut c_void>(WINDOW_STATE_IVAR);
83
84 decl.add_method(sel!(dealloc), dealloc_view as extern "C" fn(&Object, Sel));
85
86 decl.add_method(
87 sel!(keyDown:),
88 handle_view_event as extern "C" fn(&Object, Sel, id),
89 );
90 decl.add_method(
91 sel!(mouseDown:),
92 handle_view_event as extern "C" fn(&Object, Sel, id),
93 );
94 decl.add_method(
95 sel!(mouseUp:),
96 handle_view_event as extern "C" fn(&Object, Sel, id),
97 );
98 decl.add_method(
99 sel!(rightMouseDown:),
100 handle_view_event as extern "C" fn(&Object, Sel, id),
101 );
102 decl.add_method(
103 sel!(rightMouseUp:),
104 handle_view_event as extern "C" fn(&Object, Sel, id),
105 );
106 decl.add_method(
107 sel!(otherMouseDown:),
108 handle_view_event as extern "C" fn(&Object, Sel, id),
109 );
110 decl.add_method(
111 sel!(otherMouseUp:),
112 handle_view_event as extern "C" fn(&Object, Sel, id),
113 );
114 decl.add_method(
115 sel!(mouseMoved:),
116 handle_view_event as extern "C" fn(&Object, Sel, id),
117 );
118 decl.add_method(
119 sel!(mouseDragged:),
120 handle_view_event as extern "C" fn(&Object, Sel, id),
121 );
122 decl.add_method(
123 sel!(scrollWheel:),
124 handle_view_event as extern "C" fn(&Object, Sel, id),
125 );
126 decl.add_method(
127 sel!(cancelOperation:),
128 cancel_operation as extern "C" fn(&Object, Sel, id),
129 );
130
131 decl.add_method(
132 sel!(makeBackingLayer),
133 make_backing_layer as extern "C" fn(&Object, Sel) -> id,
134 );
135
136 decl.add_protocol(Protocol::get("CALayerDelegate").unwrap());
137 decl.add_method(
138 sel!(viewDidChangeBackingProperties),
139 view_did_change_backing_properties as extern "C" fn(&Object, Sel),
140 );
141 decl.add_method(
142 sel!(setFrameSize:),
143 set_frame_size as extern "C" fn(&Object, Sel, NSSize),
144 );
145 decl.add_method(
146 sel!(displayLayer:),
147 display_layer as extern "C" fn(&Object, Sel, id),
148 );
149
150 decl.register()
151 };
152}
153
154pub struct Window(Rc<RefCell<WindowState>>);
155
156struct WindowState {
157 id: usize,
158 native_window: id,
159 event_callback: Option<Box<dyn FnMut(Event)>>,
160 resize_callback: Option<Box<dyn FnMut()>>,
161 close_callback: Option<Box<dyn FnOnce()>>,
162 synthetic_drag_counter: usize,
163 executor: Rc<executor::Foreground>,
164 scene_to_render: Option<Scene>,
165 renderer: Renderer,
166 command_queue: metal::CommandQueue,
167 last_fresh_keydown: Option<(Keystroke, Option<String>)>,
168 layer: id,
169 traffic_light_position: Option<Vector2F>,
170}
171
172impl Window {
173 pub fn open(
174 id: usize,
175 options: platform::WindowOptions,
176 executor: Rc<executor::Foreground>,
177 fonts: Arc<dyn platform::FontSystem>,
178 ) -> Self {
179 const PIXEL_FORMAT: metal::MTLPixelFormat = metal::MTLPixelFormat::BGRA8Unorm;
180
181 unsafe {
182 let pool = NSAutoreleasePool::new(nil);
183
184 let frame = match options.bounds {
185 WindowBounds::Maximized => RectF::new(Default::default(), vec2f(1024., 768.)),
186 WindowBounds::Fixed(rect) => rect,
187 }
188 .to_ns_rect();
189 let mut style_mask = NSWindowStyleMask::NSClosableWindowMask
190 | NSWindowStyleMask::NSMiniaturizableWindowMask
191 | NSWindowStyleMask::NSResizableWindowMask
192 | NSWindowStyleMask::NSTitledWindowMask;
193
194 if options.titlebar_appears_transparent {
195 style_mask |= NSWindowStyleMask::NSFullSizeContentViewWindowMask;
196 }
197
198 let native_window: id = msg_send![WINDOW_CLASS, alloc];
199 let native_window = native_window.initWithContentRect_styleMask_backing_defer_(
200 frame,
201 style_mask,
202 NSBackingStoreBuffered,
203 NO,
204 );
205 assert!(!native_window.is_null());
206
207 if matches!(options.bounds, WindowBounds::Maximized) {
208 let screen = native_window.screen();
209 native_window.setFrame_display_(screen.visibleFrame(), YES);
210 }
211
212 let device =
213 metal::Device::system_default().expect("could not find default metal device");
214
215 let layer: id = msg_send![class!(CAMetalLayer), layer];
216 let _: () = msg_send![layer, setDevice: device.as_ptr()];
217 let _: () = msg_send![layer, setPixelFormat: PIXEL_FORMAT];
218 let _: () = msg_send![layer, setAllowsNextDrawableTimeout: NO];
219 let _: () = msg_send![layer, setNeedsDisplayOnBoundsChange: YES];
220 let _: () = msg_send![layer, setPresentsWithTransaction: YES];
221 let _: () = msg_send![
222 layer,
223 setAutoresizingMask: AutoresizingMask::WIDTH_SIZABLE
224 | AutoresizingMask::HEIGHT_SIZABLE
225 ];
226
227 let native_view: id = msg_send![VIEW_CLASS, alloc];
228 let native_view = NSView::init(native_view);
229 assert!(!native_view.is_null());
230
231 let window = Self(Rc::new(RefCell::new(WindowState {
232 id,
233 native_window,
234 event_callback: None,
235 resize_callback: None,
236 close_callback: None,
237 synthetic_drag_counter: 0,
238 executor,
239 scene_to_render: Default::default(),
240 renderer: Renderer::new(
241 device.clone(),
242 PIXEL_FORMAT,
243 get_scale_factor(native_window),
244 fonts,
245 ),
246 command_queue: device.new_command_queue(),
247 last_fresh_keydown: None,
248 layer,
249 traffic_light_position: options.traffic_light_position,
250 })));
251
252 (*native_window).set_ivar(
253 WINDOW_STATE_IVAR,
254 Rc::into_raw(window.0.clone()) as *const c_void,
255 );
256 native_window.setDelegate_(native_window);
257 (*native_view).set_ivar(
258 WINDOW_STATE_IVAR,
259 Rc::into_raw(window.0.clone()) as *const c_void,
260 );
261
262 if let Some(title) = options.title.as_ref() {
263 native_window.setTitle_(NSString::alloc(nil).init_str(title));
264 }
265 if options.titlebar_appears_transparent {
266 native_window.setTitlebarAppearsTransparent_(YES);
267 }
268 native_window.setAcceptsMouseMovedEvents_(YES);
269
270 native_view.setAutoresizingMask_(NSViewWidthSizable | NSViewHeightSizable);
271 native_view.setWantsBestResolutionOpenGLSurface_(YES);
272
273 // From winit crate: On Mojave, views automatically become layer-backed shortly after
274 // being added to a native_window. Changing the layer-backedness of a view breaks the
275 // association between the view and its associated OpenGL context. To work around this,
276 // on we explicitly make the view layer-backed up front so that AppKit doesn't do it
277 // itself and break the association with its context.
278 native_view.setWantsLayer(YES);
279 let _: () = msg_send![
280 native_view,
281 setLayerContentsRedrawPolicy: NSViewLayerContentsRedrawDuringViewResize
282 ];
283
284 native_window.setContentView_(native_view.autorelease());
285 native_window.makeFirstResponder_(native_view);
286
287 native_window.center();
288 native_window.makeKeyAndOrderFront_(nil);
289
290 window.0.borrow().move_traffic_light();
291 pool.drain();
292
293 window
294 }
295 }
296
297 pub fn key_window_id() -> Option<usize> {
298 unsafe {
299 let app = NSApplication::sharedApplication(nil);
300 let key_window: id = msg_send![app, keyWindow];
301 if msg_send![key_window, isKindOfClass: WINDOW_CLASS] {
302 let id = get_window_state(&*key_window).borrow().id;
303 Some(id)
304 } else {
305 None
306 }
307 }
308 }
309}
310
311impl Drop for Window {
312 fn drop(&mut self) {
313 unsafe {
314 self.0.as_ref().borrow().native_window.close();
315 }
316 }
317}
318
319impl platform::Window for Window {
320 fn as_any_mut(&mut self) -> &mut dyn Any {
321 self
322 }
323
324 fn on_event(&mut self, callback: Box<dyn FnMut(Event)>) {
325 self.0.as_ref().borrow_mut().event_callback = Some(callback);
326 }
327
328 fn on_resize(&mut self, callback: Box<dyn FnMut()>) {
329 self.0.as_ref().borrow_mut().resize_callback = Some(callback);
330 }
331
332 fn on_close(&mut self, callback: Box<dyn FnOnce()>) {
333 self.0.as_ref().borrow_mut().close_callback = Some(callback);
334 }
335
336 fn prompt(
337 &self,
338 level: platform::PromptLevel,
339 msg: &str,
340 answers: &[&str],
341 ) -> oneshot::Receiver<usize> {
342 unsafe {
343 let alert: id = msg_send![class!(NSAlert), alloc];
344 let alert: id = msg_send![alert, init];
345 let alert_style = match level {
346 platform::PromptLevel::Info => 1,
347 platform::PromptLevel::Warning => 0,
348 platform::PromptLevel::Critical => 2,
349 };
350 let _: () = msg_send![alert, setAlertStyle: alert_style];
351 let _: () = msg_send![alert, setMessageText: ns_string(msg)];
352 for (ix, answer) in answers.into_iter().enumerate() {
353 let button: id = msg_send![alert, addButtonWithTitle: ns_string(answer)];
354 let _: () = msg_send![button, setTag: ix as NSInteger];
355 }
356 let (done_tx, done_rx) = oneshot::channel();
357 let done_tx = Cell::new(Some(done_tx));
358 let block = ConcreteBlock::new(move |answer: NSInteger| {
359 if let Some(mut done_tx) = done_tx.take() {
360 let _ = postage::sink::Sink::try_send(&mut done_tx, answer.try_into().unwrap());
361 }
362 });
363 let block = block.copy();
364 let native_window = self.0.borrow().native_window;
365 let _: () = msg_send![
366 alert,
367 beginSheetModalForWindow: native_window
368 completionHandler: block
369 ];
370 done_rx
371 }
372 }
373
374 fn activate(&self) {
375 unsafe {
376 let _: () = msg_send![self.0.borrow().native_window, makeKeyAndOrderFront: nil];
377 }
378 }
379}
380
381impl platform::WindowContext for Window {
382 fn size(&self) -> Vector2F {
383 self.0.as_ref().borrow().size()
384 }
385
386 fn scale_factor(&self) -> f32 {
387 self.0.as_ref().borrow().scale_factor()
388 }
389
390 fn present_scene(&mut self, scene: Scene) {
391 self.0.as_ref().borrow_mut().present_scene(scene);
392 }
393
394 fn titlebar_height(&self) -> f32 {
395 self.0.as_ref().borrow().titlebar_height()
396 }
397}
398
399impl WindowState {
400 fn move_traffic_light(&self) {
401 if let Some(traffic_light_position) = self.traffic_light_position {
402 let titlebar_height = self.titlebar_height();
403
404 unsafe {
405 let close_button: id = msg_send![
406 self.native_window,
407 standardWindowButton: NSWindowButton::NSWindowCloseButton
408 ];
409 let min_button: id = msg_send![
410 self.native_window,
411 standardWindowButton: NSWindowButton::NSWindowMiniaturizeButton
412 ];
413 let zoom_button: id = msg_send![
414 self.native_window,
415 standardWindowButton: NSWindowButton::NSWindowZoomButton
416 ];
417
418 let mut close_button_frame: CGRect = msg_send![close_button, frame];
419 let mut min_button_frame: CGRect = msg_send![min_button, frame];
420 let mut zoom_button_frame: CGRect = msg_send![zoom_button, frame];
421 let mut origin = vec2f(
422 traffic_light_position.x(),
423 titlebar_height
424 - traffic_light_position.y()
425 - close_button_frame.size.height as f32,
426 );
427 let button_spacing =
428 (min_button_frame.origin.x - close_button_frame.origin.x) as f32;
429
430 close_button_frame.origin = CGPoint::new(origin.x() as f64, origin.y() as f64);
431 let _: () = msg_send![close_button, setFrame: close_button_frame];
432 origin.set_x(origin.x() + button_spacing);
433
434 min_button_frame.origin = CGPoint::new(origin.x() as f64, origin.y() as f64);
435 let _: () = msg_send![min_button, setFrame: min_button_frame];
436 origin.set_x(origin.x() + button_spacing);
437
438 zoom_button_frame.origin = CGPoint::new(origin.x() as f64, origin.y() as f64);
439 let _: () = msg_send![zoom_button, setFrame: zoom_button_frame];
440 }
441 }
442 }
443}
444
445impl platform::WindowContext for WindowState {
446 fn size(&self) -> Vector2F {
447 let NSSize { width, height, .. } =
448 unsafe { NSView::frame(self.native_window.contentView()) }.size;
449 vec2f(width as f32, height as f32)
450 }
451
452 fn scale_factor(&self) -> f32 {
453 get_scale_factor(self.native_window)
454 }
455
456 fn titlebar_height(&self) -> f32 {
457 unsafe {
458 let frame = NSWindow::frame(self.native_window);
459 let content_layout_rect: CGRect = msg_send![self.native_window, contentLayoutRect];
460 (frame.size.height - content_layout_rect.size.height) as f32
461 }
462 }
463
464 fn present_scene(&mut self, scene: Scene) {
465 self.scene_to_render = Some(scene);
466 unsafe {
467 let _: () = msg_send![self.native_window.contentView(), setNeedsDisplay: YES];
468 }
469 }
470}
471
472fn get_scale_factor(native_window: id) -> f32 {
473 unsafe {
474 let screen: id = msg_send![native_window, screen];
475 NSScreen::backingScaleFactor(screen) as f32
476 }
477}
478
479unsafe fn get_window_state(object: &Object) -> Rc<RefCell<WindowState>> {
480 let raw: *mut c_void = *object.get_ivar(WINDOW_STATE_IVAR);
481 let rc1 = Rc::from_raw(raw as *mut RefCell<WindowState>);
482 let rc2 = rc1.clone();
483 mem::forget(rc1);
484 rc2
485}
486
487unsafe fn drop_window_state(object: &Object) {
488 let raw: *mut c_void = *object.get_ivar(WINDOW_STATE_IVAR);
489 Rc::from_raw(raw as *mut RefCell<WindowState>);
490}
491
492extern "C" fn yes(_: &Object, _: Sel) -> BOOL {
493 YES
494}
495
496extern "C" fn dealloc_window(this: &Object, _: Sel) {
497 unsafe {
498 drop_window_state(this);
499 let () = msg_send![super(this, class!(NSWindow)), dealloc];
500 }
501}
502
503extern "C" fn dealloc_view(this: &Object, _: Sel) {
504 unsafe {
505 drop_window_state(this);
506 let () = msg_send![super(this, class!(NSView)), dealloc];
507 }
508}
509
510extern "C" fn handle_view_event(this: &Object, _: Sel, native_event: id) {
511 let window_state = unsafe { get_window_state(this) };
512 let weak_window_state = Rc::downgrade(&window_state);
513 let mut window_state_borrow = window_state.as_ref().borrow_mut();
514
515 let event = unsafe { Event::from_native(native_event, Some(window_state_borrow.size().y())) };
516
517 if let Some(event) = event {
518 match &event {
519 Event::LeftMouseDragged { position } => {
520 window_state_borrow.synthetic_drag_counter += 1;
521 window_state_borrow
522 .executor
523 .spawn(synthetic_drag(
524 weak_window_state,
525 window_state_borrow.synthetic_drag_counter,
526 *position,
527 ))
528 .detach();
529 }
530 Event::LeftMouseUp { .. } => {
531 window_state_borrow.synthetic_drag_counter += 1;
532 }
533
534 // Ignore events from held-down keys after some of the initially-pressed keys
535 // were released.
536 Event::KeyDown {
537 input,
538 keystroke,
539 is_held,
540 } => {
541 let keydown = (keystroke.clone(), input.clone());
542 if *is_held {
543 if window_state_borrow.last_fresh_keydown.as_ref() != Some(&keydown) {
544 return;
545 }
546 } else {
547 window_state_borrow.last_fresh_keydown = Some(keydown);
548 }
549 }
550
551 _ => {}
552 }
553
554 if let Some(mut callback) = window_state_borrow.event_callback.take() {
555 drop(window_state_borrow);
556 callback(event);
557 window_state.borrow_mut().event_callback = Some(callback);
558 }
559 }
560}
561
562// Allows us to receive `cmd-.` (the shortcut for closing a dialog)
563// https://bugs.eclipse.org/bugs/show_bug.cgi?id=300620#c6
564extern "C" fn cancel_operation(this: &Object, _sel: Sel, _sender: id) {
565 let window_state = unsafe { get_window_state(this) };
566 let mut window_state_borrow = window_state.as_ref().borrow_mut();
567
568 let chars = ".".to_string();
569 let keystroke = Keystroke {
570 cmd: true,
571 ctrl: false,
572 alt: false,
573 shift: false,
574 key: chars.clone(),
575 };
576 let event = Event::KeyDown {
577 keystroke: keystroke.clone(),
578 input: Some(chars.clone()),
579 is_held: false,
580 };
581
582 window_state_borrow.last_fresh_keydown = Some((keystroke, Some(chars)));
583 if let Some(mut callback) = window_state_borrow.event_callback.take() {
584 drop(window_state_borrow);
585 callback(event);
586 window_state.borrow_mut().event_callback = Some(callback);
587 }
588}
589
590extern "C" fn send_event(this: &Object, _: Sel, native_event: id) {
591 unsafe {
592 let () = msg_send![super(this, class!(NSWindow)), sendEvent: native_event];
593 }
594}
595
596extern "C" fn window_did_resize(this: &Object, _: Sel, _: id) {
597 let window_state = unsafe { get_window_state(this) };
598 window_state.as_ref().borrow().move_traffic_light();
599}
600
601extern "C" fn close_window(this: &Object, _: Sel) {
602 unsafe {
603 let close_callback = {
604 let window_state = get_window_state(this);
605 window_state
606 .as_ref()
607 .try_borrow_mut()
608 .ok()
609 .and_then(|mut window_state| window_state.close_callback.take())
610 };
611
612 if let Some(callback) = close_callback {
613 callback();
614 }
615
616 let () = msg_send![super(this, class!(NSWindow)), close];
617 }
618}
619
620extern "C" fn make_backing_layer(this: &Object, _: Sel) -> id {
621 let window_state = unsafe { get_window_state(this) };
622 let window_state = window_state.as_ref().borrow();
623 window_state.layer
624}
625
626extern "C" fn view_did_change_backing_properties(this: &Object, _: Sel) {
627 let window_state = unsafe { get_window_state(this) };
628 let mut window_state_borrow = window_state.as_ref().borrow_mut();
629
630 unsafe {
631 let _: () = msg_send![window_state_borrow.layer, setContentsScale: window_state_borrow.scale_factor() as f64];
632 }
633
634 if let Some(mut callback) = window_state_borrow.resize_callback.take() {
635 drop(window_state_borrow);
636 callback();
637 window_state.as_ref().borrow_mut().resize_callback = Some(callback);
638 };
639}
640
641extern "C" fn set_frame_size(this: &Object, _: Sel, size: NSSize) {
642 let window_state = unsafe { get_window_state(this) };
643 let mut window_state_borrow = window_state.as_ref().borrow_mut();
644
645 if window_state_borrow.size() == vec2f(size.width as f32, size.height as f32) {
646 return;
647 }
648
649 unsafe {
650 let _: () = msg_send![super(this, class!(NSView)), setFrameSize: size];
651 }
652
653 let scale_factor = window_state_borrow.scale_factor() as f64;
654 let drawable_size: NSSize = NSSize {
655 width: size.width * scale_factor,
656 height: size.height * scale_factor,
657 };
658
659 unsafe {
660 let _: () = msg_send![window_state_borrow.layer, setDrawableSize: drawable_size];
661 }
662
663 if let Some(mut callback) = window_state_borrow.resize_callback.take() {
664 drop(window_state_borrow);
665 callback();
666 window_state.borrow_mut().resize_callback = Some(callback);
667 };
668}
669
670extern "C" fn display_layer(this: &Object, _: Sel, _: id) {
671 unsafe {
672 let window_state = get_window_state(this);
673 let mut window_state = window_state.as_ref().borrow_mut();
674
675 if let Some(scene) = window_state.scene_to_render.take() {
676 let drawable: &metal::MetalDrawableRef = msg_send![window_state.layer, nextDrawable];
677 let command_queue = window_state.command_queue.clone();
678 let command_buffer = command_queue.new_command_buffer();
679
680 let size = window_state.size();
681 let scale_factor = window_state.scale_factor();
682
683 window_state.renderer.render(
684 &scene,
685 size * scale_factor,
686 command_buffer,
687 drawable.texture(),
688 );
689
690 command_buffer.commit();
691 command_buffer.wait_until_completed();
692 drawable.present();
693 };
694 }
695}
696
697async fn synthetic_drag(
698 window_state: Weak<RefCell<WindowState>>,
699 drag_id: usize,
700 position: Vector2F,
701) {
702 loop {
703 Timer::after(Duration::from_millis(16)).await;
704 if let Some(window_state) = window_state.upgrade() {
705 let mut window_state_borrow = window_state.borrow_mut();
706 if window_state_borrow.synthetic_drag_counter == drag_id {
707 if let Some(mut callback) = window_state_borrow.event_callback.take() {
708 drop(window_state_borrow);
709 callback(Event::LeftMouseDragged { position });
710 window_state.borrow_mut().event_callback = Some(callback);
711 }
712 } else {
713 break;
714 }
715 }
716 }
717}
718
719unsafe fn ns_string(string: &str) -> id {
720 NSString::alloc(nil).init_str(string).autorelease()
721}