ASRock E350M1 - FreeBSD

Hardware info on main page.

Internal drives:

ada0 (linux: sda) - 60 GB OCZ Agility 3 SSD - FreeBSD

root@kg-f4# gpart show -p ada0
=>       34  117231341    ada0  GPT  (55G)
         34        128  ada0p1  freebsd-boot   (64k)
        162   54525952  ada0p2  freebsd-ufs    (26G) RELENG_9, currently FreeBSD 9.3-stable
   54526114    8388608  ada0p3  freebsd-swap  (4.0G)
   62914722   52428800  ada0p4  freebsd-ufs    (25G)
  115343522    1887853          - free -      (921M)

ada1 (linux: sdb) - 60 GB OCZ Agility 3 SSD - Xubuntu

root@kg-f4# gpart show -p ada1
=>       34  117231341    ada1  GPT  (55G)
         34       2014          - free -      (1M)
       2048       2048  ada1p1  bios-boot   (1.0M)
       4096   58632813  ada1p2  linux-data   (28G) Xubuntu 12.04 LTS (standard)
   58636909    7812501  ada1p3  linux-swap  (3.7G)
   66449410       2046          - free -      (1M)
   66451456   24576000  ada1p4  linux-data   (11G) Xubuntu 11.10
   91027456   26202112  ada1p5  linux-data   (12G) Xubuntu 12.04 LTS (modified)
  117229568       1807          - free -    (903k)

external hard drive

da0 (linux: sdc) - 1 TB Samsung HN-M101MBB drive, used for scratch storage (connected via sata-to-usb adapter)

root@kg-f4# gpart show -p da0
=>        34  1953525101    da0  GPT  (931G)
          34   209715200  da0p1  linux-data  (100G)
   209715234   314572800  da0p2  linux-data  (150G)
   524288034  1429237101         - free -  (681G)

old external hard drive (da0, 60 GB, yellow sticker that says "f3") connected through a sata docking to usb adapter.

da0s1 - FreeBSD 8.2-stable (RELENG_8)
da0s2 - FreeBSD 9.0-RC1 (RELENG_9)

older external hard drive sdc (20 GB, Hitachi IDE, connected via usb-to-IDE adapter)

sdc1 - Xubuntu 11.10

Work log

2016-03-10: ada0p2 - to configure tvheadend, I ran it for the first time with

tvheadend_flags="-C"

in /etc/rc.conf, then I commented it out and restarted tvheadend.

2016-03-10: ada0p2 - ports - install tvheadend:

Mar 10 18:35:34 kg-f4 pkg-static: m4-1.4.17_1,1 installed
Mar 10 18:48:17 kg-f4 pkg-static: perl5-5.20.3_8 installed
Mar 10 18:49:19 kg-f4 pkg-static: bison-2.7.1,1 installed
Mar 10 18:50:26 kg-f4 pkg-static: bash-4.3.42_1 installed
Mar 10 18:51:01 kg-f4 pkg-static: libffi-3.2.1 installed
Mar 10 18:55:10 kg-f4 pkg-static: python27-2.7.11_1 installed
Mar 10 22:46:28 kg-f4 pkg-static: ca_root_nss-3.22.2 installed
Mar 10 22:46:32 kg-f4 pkg-static: curl-7.47.1 installed
Mar 10 22:46:52 kg-f4 pkg-static: uriparser-0.8.4 installed
Mar 10 22:47:04 kg-f4 pkg-static: libdvbcsa-1.1.0_1 installed
Mar 10 22:47:10 kg-f4 pkg-static: libhdhomerun-20150826 installed
Mar 10 22:47:18 kg-f4 pkg-static: libexecinfo-1.1_3 installed
Mar 10 22:48:50 kg-f4 pkg-static: dtv-scan-tables-20140612 installed
Mar 10 22:48:56 kg-f4 pkg-static: tvheadend-4.0.8_1 installed

ok.

2016-03-10: ada0p2 - ports - install webcamd:

Mar 10 18:16:14 kg-f4 pkg-static: pkg-1.6.4_1 installed
Mar 10 18:16:27 kg-f4 pkg-static: v4l_compat-1.6.3 installed
Mar 10 18:16:30 kg-f4 pkg-static: dialog4ports-0.1.5_2 installed
Mar 10 18:17:14 kg-f4 pkg-static: cuse4bsd-kmod-0.1.36 installed
Mar 10 18:17:19 kg-f4 pkg-static: pkgconf-0.9.12_1 installed
Mar 10 18:18:38 kg-f4 pkg-static: libiconv-1.14_9 installed
Mar 10 18:19:19 kg-f4 pkg-static: indexinfo-0.2.4 installed
Mar 10 18:19:21 kg-f4 pkg-static: gettext-runtime-0.19.7 installed
Mar 10 18:24:48 kg-f4 pkg-static: gettext-tools-0.19.7 installed
Mar 10 18:25:06 kg-f4 pkg-static: gmake-4.1_2 installed
Mar 10 18:27:36 kg-f4 pkg-static: nasm-2.11.08_1,1 installed
Mar 10 18:28:15 kg-f4 pkg-static: jpeg-turbo-1.4.2 installed
Mar 10 18:28:56 kg-f4 pkg-static: libv4l-1.6.3_1 installed
Mar 10 18:31:40 kg-f4 pkg-static: webcamd-4.2.0.9 installed

ok.

2016-03-10: ada0p2 - ports - get an updated ports tree onto the machine via portsnap fetch; portsnap update.

2016-03-10: ada0p2 - deinstall all packages (= ports). It is easier to start from scratch here, with a fresh ports tree.

root@kg-f4# pkg_deinstall -a
--->  Deinstalling 'xfce-4.10_6'
--->  Deinstalling 'xfce4-mixer-4.10.0_4'
[Updating the pkgdb <format:bdb_btree> in /var/db/pkg ... - 404 packages found (-1 +0) (...) done]
[...]
--->  Deinstalling 'libiconv-1.14_1'
[Updating the pkgdb <format:bdb_btree> in /var/db/pkg ... - 1 packages found (-1 +0) (...) done]
pkg_delete: file '/usr/local/lib/charset.alias' doesn't exist
pkg_delete: couldn't entirely delete package `libiconv-1.14_1'
(perhaps the packing list is incorrectly specified?)
[Updating the pkgdb <format:bdb_btree> in /var/db/pkg ... - 0 packages found (-1 +0)  nothing to do]

ok.

2016-03-10: ada0p2 - stop some services

root@kg-f4# service tvheadend stop
Stopping tvheadend.
Waiting for PIDS: 561.
root@kg-f4# service webcamd stop

ok.

2016-03-10: ada0p2 - a reboot later, the machine runs FreeBSD 9.3-stable. dmesg output: normal, verbose.

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.3-STABLE FreeBSD 9.3-STABLE #4 r296579: Thu Mar 10 09:28:13 CET 2016     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

ok.

2016-03-10: ada0p2 - "make world" continues. kernel

root@kg-f4# make kernel
[...]
===> zlib (install)
install -o root -g wheel -m 555   zlib.ko /boot/kernel
install -o root -g wheel -m 555   zlib.ko.symbols /boot/kernel
kldxref /boot/kernel

I'll do the rest in multiuser too. mergemaster pre

root@kg-f4# mergemaster -p

*** Creating the temporary root environment in /var/tmp/temproot
 *** /var/tmp/temproot ready for use
 *** Creating and populating directory structure in /var/tmp/temproot
[...]
*** Comparison complete

*** /var/tmp/temproot is empty, deleting

install world

root@kg-f4# make installworld
[...]
install -s -o root -g wheel -m 555   ldd32 /usr/bin/ldd32

delete old stuff

root@kg-f4# make delete-old
>>> Removing old files (only deletes safe to delete libs)
remove /usr/share/man/man9/MEXT_ADD_REF.9.gz? y
remove /usr/share/man/man9/MEXTFREE.9.gz? y
remove /usr/share/man/man9/MEXT_IS_REF.9.gz? y
remove /usr/share/man/man9/MEXT_REM_REF.9.gz? y
remove /usr/share/man/man9/MFREE.9.gz? y
remove /usr/bin/sgsmsg? y
remove /usr/share/man/man9/sleepq_calc_signal_retval.9.gz? y
remove /usr/share/man/man9/sleepq_catch_signals.9.gz? y
remove /usr/share/man/man9/VOP_GETVOBJECT.9.gz? y
remove /usr/share/man/man9/VOP_CREATEVOBJECT.9.gz? y
remove /usr/share/man/man9/VOP_DESTROYVOBJECT.9.gz? y
remove /usr/bin/sendbug? y
remove /usr/share/info/send-pr.info.gz? y
remove /usr/share/man/man1/send-pr.1.gz? y
remove /usr/share/man/man1/sendbug.1.gz? y
remove /etc/gnats/freefall? y
remove /usr/include/clang/3.3/__wmmintrin_aes.h? y
remove /usr/include/clang/3.3/__wmmintrin_pclmul.h? y
remove /usr/include/clang/3.3/altivec.h? y
remove /usr/include/clang/3.3/ammintrin.h? y
remove /usr/include/clang/3.3/avx2intrin.h? y
remove /usr/include/clang/3.3/avxintrin.h? y
remove /usr/include/clang/3.3/bmi2intrin.h? y
remove /usr/include/clang/3.3/bmiintrin.h? y
remove /usr/include/clang/3.3/cpuid.h? y
remove /usr/include/clang/3.3/emmintrin.h? y
remove /usr/include/clang/3.3/f16cintrin.h? y
remove /usr/include/clang/3.3/fma4intrin.h? y
remove /usr/include/clang/3.3/fmaintrin.h? y
remove /usr/include/clang/3.3/immintrin.h? y
remove /usr/include/clang/3.3/lzcntintrin.h? y
remove /usr/include/clang/3.3/mm3dnow.h? y
remove /usr/include/clang/3.3/mm_malloc.h? y
remove /usr/include/clang/3.3/mmintrin.h? y
remove /usr/include/clang/3.3/module.map? y
remove /usr/include/clang/3.3/nmmintrin.h? y
remove /usr/include/clang/3.3/pmmintrin.h? y
remove /usr/include/clang/3.3/popcntintrin.h? y
remove /usr/include/clang/3.3/prfchwintrin.h? y
remove /usr/include/clang/3.3/rdseedintrin.h? y
remove /usr/include/clang/3.3/rtmintrin.h? y
remove /usr/include/clang/3.3/smmintrin.h? y
remove /usr/include/clang/3.3/tmmintrin.h? y
remove /usr/include/clang/3.3/wmmintrin.h? y
remove /usr/include/clang/3.3/x86intrin.h? y
remove /usr/include/clang/3.3/xmmintrin.h? y
remove /usr/include/clang/3.3/xopintrin.h? y
remove /usr/lib/libssh.a? y
remove /usr/lib/libssh.so? y
remove /usr/lib/libssh_p.a? y
remove /usr/lib32/libssh.a? y
remove /usr/lib32/libssh.so? y
remove /usr/lib32/libssh_p.a? y
remove /usr/libexec/bsdconfig/070.usermgmt/userinput? y
remove /usr/libexec/bsdconfig/070.usermgmt/groupinput? y
>>> Old files removed
>>> Removing old directories
/usr/share/examples/iscsi
/etc/gnats
/usr/include/clang/3.3
/usr/share/examples/netgraph/bluetooth
/usr/include/c++/v1/experimental
/usr/include/c++/v1/ext
rmdir: /usr/include/c++/v1: Directory not empty
>>> Old directories removed
To remove old libraries run '/usr/obj/usr/src/make.amd64/make delete-old-libs'.
root@kg-f4# make delete-old-libs
>>> Removing old libraries
Please be sure no application still uses those libraries, else you
can not start such an application. Consult UPDATING for more
information regarding how to cope with the removal/revision bump
of a specific library.
remove /usr/lib/libssh.so.5? y
remove /usr/lib32/libssh.so.5? y
>>> Old libraries removed

mergemaster

root@kg-f4# mergemaster -iUP
[...]
*** You chose the automatic install option for files that did not
    exist on your system.  The following were installed for you:
      /etc/devd/zfs.conf
      /etc/libmap32.conf
      /etc/ntp/leap-seconds
      /etc/periodic/daily/480.leapfile-ntpd
      /etc/periodic/daily/510.status-world-kernel
      /etc/pkg/FreeBSD.conf


*** You chose the automatic upgrade option for files that you did
    not alter on your system.  The following were upgraded for you:
      /COPYRIGHT
      /boot/device.hints
      /etc/defaults/periodic.conf
      /etc/defaults/rc.conf
      /etc/devd.conf
      /etc/devd/usb.conf
      /etc/inetd.conf
      /etc/mail/freebsd.cf
      /etc/mail/freebsd.mc
      /etc/mail/freebsd.submit.cf
      /etc/mail/freebsd.submit.mc
      /etc/mail/helpfile
      /etc/mail/sendmail.cf
      /etc/mail/submit.cf
      /etc/mtree/BSD.include.dist
      /etc/mtree/BSD.root.dist
      /etc/mtree/BSD.usr.dist
      /etc/mtree/BSD.var.dist
      /etc/network.subr
      /etc/newsyslog.conf
      /etc/pam.d/README
      /etc/periodic/daily/110.clean-tmps
      /etc/periodic/daily/420.status-network
      /etc/periodic/daily/800.scrub-zfs
      /etc/periodic/security/800.loginfail
      /etc/portsnap.conf
      /etc/rc.d/devd
      /etc/rc.d/fsck
      /etc/rc.d/jail
      /etc/rc.d/mdconfig
      /etc/rc.d/mdconfig2
      /etc/rc.d/ntpd
      /etc/rc.d/sshd
      /etc/rc.d/syslogd
      /etc/rc.d/ugidfw
      /etc/rc.subr
      /etc/services
      /etc/ssh/moduli
      /etc/ssh/ssh_config
      /etc/ssh/sshd_config
      /etc/ttys
      /var/named/etc/namedb/named.root

*** You installed a services file, so make sure that you run
    '/usr/sbin/services_mkdb -q -o /var/db/services.db /etc/services'
     to rebuild your services database

    Would you like to run it now? y or n [n] y
    Running /usr/sbin/services_mkdb -q -o /var/db/services.db /etc/services


*** Reinstalling Europe/Oslo as /etc/localtime

ok.

2016-03-09: ada0p2 - build latest FreeBSD 9.3-stable via "make world".

root@kg-f4# pwd
/usr/src

build world

root@kg-f4# make -j4 buildworld
[...]
--------------------------------------------------------------
>>> World build completed on Thu Mar 10 02:01:28 CET 2016
--------------------------------------------------------------

ok.

2016-03-09: ada0p2 - update source to latest RELENG_9:

root@kg-f4# cd /usr/src
root@kg-f4# svn up
svn: E155036: Please see the 'svn upgrade' command
svn: E155036: The working copy at '/usr/src'
is too old (format 29) to work with client version '1.8.5 (r1542147)' (expects format 31). You need to upgrade the working copy first.

ok

root@kg-f4# svn upgrade
Upgraded '.'

then

root@kg-f4# svn up
[...]
 U   rescue
UU   MAINTAINERS
 U   .
Updated to revision 296579.

check

root@kg-f4# egrep "^BRANCH|^REVISION" /usr/src/sys/conf/newvers.sh
REVISION="9.3"
BRANCH="STABLE"

good.

2016-03-09: ada0p2 - I booted FreeBSD. Still running

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.2-STABLE FreeBSD 9.2-STABLE #3 r261516: Wed Feb  5 22:38:36 CET 2014     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

time for an upgrade. Before that, check interesting processes running:

root@kg-f4# pgrep -lf webcamd
802 /usr/local/bin/tvheadend -f -p /var/run/tvheadend.pid -u webcamd -g webcamd -c /usr/local/etc/tvheadend
530 /usr/local/sbin/webcamd -B -U webcamd -G webcamd -d ugen3.3 -i 0
488 /usr/local/sbin/webcamd -B -U webcamd -G webcamd -d ugen3.2 -i 0

nice. Interesting things in /var/log/messages:

Mar  9 20:37:44 kg-f4 tvheadend[802]: dvr: Output directory for video recording is not yet configured for DVR configuration "". Defaulting to to "/var/empty". This can be changed from the web user interface.
Mar  9 20:37:44 kg-f4 tvheadend[802]: START: HTS Tvheadend version 0.0.0~unknown started, running as PID:802 UID:145 GID:145, CWD:/ CNF:/usr/local/etc/tvheadend

interesting ports installed:

cuse4bsd-kmod-0.1.30_1      =  up-to-date with port
tvheadend-3.9.20140212      >  succeeds port (port has 3.4.0.20130726.3_5)
w_scan-20120415             =  up-to-date with port
webcamd-3.11.0.2            =  up-to-date with port

contents of /boot/loader.conf

root@kg-f4# more /boot/loader.conf
amdtemp_load="YES"
cuse4bsd_load="YES"
/etc/rc.conf contents
root@kg-f4# more /etc/rc.conf
hostname="kg-f4.kg4.no"
keymap="norwegian.iso.kbd"
ifconfig_re0="DHCP"
sshd_enable="YES"
moused_enable="YES"
saver="blank"
ntpd_enable="YES"
# Set dumpdev to "AUTO" to enable crash dumps, "NO" to disable
dumpdev="AUTO"
# enable linux kernel module
linux_enable="YES"
# smartd
smartd_enable="YES"
# dbus
dbus_enable="YES"
# webcamd
webcamd_enable="YES"
# tvheadend
tvheadend_enable="YES"
#tvheadend_flags="-C"

ok.

2014-02-15: ada0p2 - I added

cuse4bsd_load="YES"

to /boot/loader.conf so that cuse4bsd will load automatically on boot.

2014-02-15: ada0p2 - ports - I built tvheadend with default parameters:

root@kg-f4# cd /usr/ports/multimedia/tvheadend
root@kg-f4# make showconfig
===> The following configuration options are available for tvheadend-3.4.0.20130726.3_5:
     AVAHI=off: Zeroconf support via Avahi
     DVBCSA=on: Replace internal ffdecsa with dvbcsa
===> Use 'make config' to modify these settings

port installation message:

============================================================================

For the first start in your /etc/rc.conf:
  tvheadend_enable="YES"
  tvheadend_flags="-C"

The second line can be removed after the first start.

Patches, feedback and help are always welcome!

============================================================================

Let's see if it works. I input the necessary parameters in rc.conf, switch the the PCTV stick (in a different terminal):

root@kg-f4# usbconfig -d ugen3.3

start webcamd:

root@kg-f4# service webcamd start ugen3.3
Starting webcamd.
Attached to ugen3.3[0]

check devices:

root@kg-f4# ls -l /dev/dvb
total 1
dr-xr-xr-x  2 root  wheel  512 Feb 15 10:56 adapter0
root@kg-f4# ls -l /dev/dvb/*
total 0
crw-rw----  1 webcamd  webcamd  0x9d Feb 15 10:55 demux0
crw-rw----  1 webcamd  webcamd  0x9e Feb 15 10:55 dvr0
crw-rw----  1 webcamd  webcamd  0x9f Feb 15 10:55 frontend0

good. and then start tvheadend:

root@kg-f4# service tvheadend start
Starting tvheadend.

First, go to admin web (hostname:9981/) and set security.

2014-02-15: ada0p2 - ports - I upgraded ports again, with portsnap fetch; portsnap update.

2014-02-11: ada0p2 - ports - on the mailing list, the maintainer confirmed that the tvheadend port was broken (thread) , and that he has fixed it as best he could.

2014-02-09: ada0p2 - ports - all ports updated. I also tried to install the tvheadend port. First try with default parameters failed: parameters:

root@kg-f4# cd /usr/ports/multimedia/tvheadend
root@kg-f4# make showconfig
===> The following configuration options are available for tvheadend-3.4.0.20130726.3_4:
     AVAHI=off: Zeroconf support via Avahi
     DVBCSA=on: Replace internal ffdecsa with dvbcsa
     FFMPEG=on: FFmpeg support (WMA, AIFF, AC3, APE...)
===> Use 'make config' to modify these settings

build output:

===> Fetching all distfiles required by tvheadend-3.4.0.20130726.3_4 for building
===>  Extracting for tvheadend-3.4.0.20130726.3_4
=> SHA256 Checksum OK for tvheadend-3.4.0.20130726.3.tar.gz.
=> SHA256 Checksum OK for dvb-scan-tables-20130714.tar.gz.
===>  Patching for tvheadend-3.4.0.20130726.3_4
===>  Applying FreeBSD patches for tvheadend-3.4.0.20130726.3_4
===>   tvheadend-3.4.0.20130726.3_4 depends on executable: bash - found
===>   tvheadend-3.4.0.20130726.3_4 depends on file: /usr/local/include/linux/videodev2.h - found
===>   tvheadend-3.4.0.20130726.3_4 depends on file: /usr/local/bin/python2.7 - found
===>   tvheadend-3.4.0.20130726.3_4 depends on executable: pkgconf - found
===>   tvheadend-3.4.0.20130726.3_4 depends on executable: gmake - found
===>   tvheadend-3.4.0.20130726.3_4 depends on shared library: libexecinfo.so - found
===>   tvheadend-3.4.0.20130726.3_4 depends on shared library: libcurl.so - found
===>  Configuring for tvheadend-3.4.0.20130726.3_4
Checking support/features
  checking for cc execinfo.h ...                    ok
  checking for cc -mmmx ...                         ok
  checking for cc -msse2 ...                        ok
  checking for cc getloadavg ...                    ok
  checking for cc atomic64 ...                      ok
  checking for py module gzip ...                   ok
  checking for bzip2 ...                            ok
  checking for pkg avahi-client  ...                ok
  checking for pkg libavcodec <=55.0.0 ...          fail
  checking for cc sys/inotify.h ...                 fail
  checking for pkg libcurl  ...                     ok
Package /usr/ports/packages was not found in the pkg-config search path.
Perhaps you should add the directory containing `/usr/ports/packages.pc'
to the PKG_CONFIG_PATH environment variable
Package '/usr/ports/packages', required by 'world', not found
Package /usr/ports/packages was not found in the pkg-config search path.
Perhaps you should add the directory containing `/usr/ports/packages.pc'
to the PKG_CONFIG_PATH environment variable
Package '/usr/ports/packages', required by 'world', not found

Compiler:
  Using C compiler:                        cc
  Using C flags:                           -O2 -pipe -I/usr/local/include -Wno-conversion -Wno-int-to-pointer-cast -fno-strict-aliasing
  Build for arch:                          amd64

Binaries:
  Using PYTHON:                            /usr/local/bin/python2.7

Options:
  cwc                                      yes
  v4l                                      yes
  linuxdvb                                 yes
  dvbscan                                  no
  timeshift                                yes
  trace                                    yes
  imagecache                               yes
  avahi                                    yes
  zlib                                     no
  libav                                    no
  inotify                                  no
  bundle                                   no
  dvbcsa                                   no
  epoll                                    no
  kqueue                                   yes
  execinfo                                 yes
  mmx                                      yes
  sse2                                     yes
  getloadavg                               yes
  atomic64                                 yes
  py_gzip                                  yes
  bin_bzip2                                yes
  ssl                                      yes

Packages:
Package /usr/ports/packages was not found in the pkg-config search path.
Perhaps you should add the directory containing `/usr/ports/packages.pc'
to the PKG_CONFIG_PATH environment variable
Package '/usr/ports/packages', required by 'world', not found
  /usr/ports/packages                     
  avahi-client                             0.6.31
  libcurl                                  7.34.0

Installation paths:
  Prefix:                                  /usr/local
  Binaries:                                ${prefix}/bin
  Libraries:                               ${prefix}/lib
  Data files:                              ${prefix}/share
  Man pages:                               /usr/local/man

Final Binary:
  /usr/ports/multimedia/tvheadend/work/decke-tvheadend-8a8c1a8/build.freebsd/tvheadend

Tvheadend Data Directory:
  /usr/local/share/tvheadend

===>  Building for tvheadend-3.4.0.20130726.3_4
CC              src/version.o
CC              src/main.o
CC              src/tvhlog.o
CC              src/utils.o
CC              src/wrappers.o
CC              src/access.o
CC              src/dtable.o
CC              src/tcp.o
CC              src/http.o
CC              src/notify.o
CC              src/file.o
CC              src/epg.o
CC              src/epgdb.o
CC              src/epggrab.o
CC              src/spawn.o
CC              src/packet.o
CC              src/streaming.o
CC              src/teletext.o
CC              src/channels.o
CC              src/subscriptions.o
CC              src/service.o
CC              src/psi.o
CC              src/parsers.o
CC              src/parser_h264.o
CC              src/parser_latm.o
CC              src/tsdemux.o
CC              src/bitstream.o
CC              src/htsp_server.o
CC              src/serviceprobe.o
CC              src/htsmsg.o
CC              src/htsmsg_binary.o
CC              src/htsmsg_json.o
CC              src/htsmsg_xml.o
CC              src/misc/dbl.o
CC              src/misc/json.o
CC              src/settings.o
CC              src/htsbuf.o
CC              src/trap.o
CC              src/avg.o
CC              src/htsstr.o
CC              src/rawtsinput.o
CC              src/iptv_input.o
CC              src/avc.o
CC              src/huffman.o
CC              src/filebundle.o
CC              src/config2.o
CC              src/lang_codes.o
CC              src/lang_str.o
CC              src/imagecache.o
CC              src/tvhtime.o
CC              src/tvhpoll.o
CC              src/epggrab/module.o
CC              src/epggrab/channel.o
CC              src/epggrab/module/pyepg.o
CC              src/epggrab/module/xmltv.o
CC              src/plumbing/tsfix.o
CC              src/plumbing/globalheaders.o
CC              src/dvr/dvr_db.o
CC              src/dvr/dvr_rec.o
CC              src/dvr/dvr_autorec.o
CC              src/webui/webui.o
CC              src/webui/comet.o
CC              src/webui/extjs.o
CC              src/webui/simpleui.o
CC              src/webui/statedump.o
CC              src/webui/html.o
CC              src/muxer.o
CC              src/muxer/muxer_pass.o
CC              src/muxer/muxer_tvh.o
CC              src/muxer/tvh/ebml.o
CC              src/muxer/tvh/mkmux.o
CC              src/epggrab/otamux.o
CC              src/epggrab/module/eit.o
CC              src/epggrab/module/opentv.o
CC              src/epggrab/support/freesat_huffman.o
CC              src/timeshift.o
CC              src/timeshift/timeshift_filemgr.o
CC              src/timeshift/timeshift_writer.o
CC              src/timeshift/timeshift_reader.o
CC              src/dvb/dvb.o
CC              src/dvb/dvb_support.o
CC              src/dvb/dvb_charset.o
CC              src/dvb/dvb_fe.o
CC              src/dvb/dvb_tables.o
CC              src/dvb/diseqc.o
CC              src/dvb/dvb_adapter.o
CC              src/dvb/dvb_multiplex.o
CC              src/dvb/dvb_service.o
CC              src/dvb/dvb_preconf.o
CC              src/dvb/dvb_satconf.o
CC              src/dvb/dvb_input_filtered.o
CC              src/dvb/dvb_input_raw.o
CC              src/webui/extjs_dvb.o
CC              src/muxes.o
CC              src/v4l.o
CC              src/webui/extjs_v4l.o
CC              src/avahi.o
CC              src/cwc.o
CC              src/capmt.o
CC              src/ffdecsa/ffdecsa_interface.o
CC              src/ffdecsa/ffdecsa_int.o
CC              src/ffdecsa/ffdecsa_mmx.o
CC              src/ffdecsa/ffdecsa_sse2.o
In file included from src/ffdecsa/ffdecsa_sse2.c:2:
src/ffdecsa/FFdecsa.c: In function 'block_decypher_group':
src/ffdecsa/FFdecsa.c:407: note: use -flax-vector-conversions to permit conversions between vectors with differing element types or numbers of subparts
src/ffdecsa/FFdecsa.c:407: error: incompatible type for argument 1 of '__builtin_ia32_psrlqi128'
src/ffdecsa/FFdecsa.c:407: error: incompatible type for argument 1 of '__builtin_ia32_psrlqi128'
src/ffdecsa/FFdecsa.c:407: error: incompatible type for argument 1 of '__builtin_ia32_psrlqi128'
gmake: *** [/usr/ports/multimedia/tvheadend/work/decke-tvheadend-8a8c1a8/build.freebsd/src/ffdecsa/ffdecsa_sse2.o] Error 1
*** [do-build] Error code 1

Stop in /usr/ports/multimedia/tvheadend.
*** [build] Error code 1

Stop in /usr/ports/multimedia/tvheadend.
** Command failed [exit code 1]: /usr/bin/script -qa /tmp/portinstall20140209-77470-whkcdq env make
** Fix the problem and try again.
** Listing the failed packages (-:ignored / *:skipped / !:failed)
    ! multimedia/tvheadend    (compiler error)

Next try, parameters changed:

root@kg-f4# make showconfig
===> The following configuration options are available for tvheadend-3.4.0.20130726.3_4:
     AVAHI=off: Zeroconf support via Avahi
     DVBCSA=off: Replace internal ffdecsa with dvbcsa
     FFMPEG=on: FFmpeg support (WMA, AIFF, AC3, APE...)
===> Use 'make config' to modify these settings

build

root@kg-f4# make
/!\ WARNING /!\
pkg_install EOL is scheduled for 2014-09-01. Please consider migrating to pkgng
http://blogs.freebsdish.org/portmgr/2014/02/03/time-to-bid-farewell-to-the-old-pkg_-tools/
If you do not want to see this message again set NO_WARNING_PKG_INSTALL_EOL=yes in your make.conf

===>  License GPLv3 accepted by the user
===>  Found saved configuration for tvheadend-3.4.0.20130726.3_4
===> Fetching all distfiles required by tvheadend-3.4.0.20130726.3_4 for building
===>  Extracting for tvheadend-3.4.0.20130726.3_4
=> SHA256 Checksum OK for tvheadend-3.4.0.20130726.3.tar.gz.
=> SHA256 Checksum OK for dvb-scan-tables-20130714.tar.gz.
===>  Patching for tvheadend-3.4.0.20130726.3_4
===>  Applying FreeBSD patches for tvheadend-3.4.0.20130726.3_4
===>   tvheadend-3.4.0.20130726.3_4 depends on executable: bash - found
===>   tvheadend-3.4.0.20130726.3_4 depends on file: /usr/local/include/linux/videodev2.h - found
===>   tvheadend-3.4.0.20130726.3_4 depends on file: /usr/local/bin/python2.7 - found
===>   tvheadend-3.4.0.20130726.3_4 depends on executable: pkgconf - found
===>   tvheadend-3.4.0.20130726.3_4 depends on executable: gmake - found
===>   tvheadend-3.4.0.20130726.3_4 depends on shared library: libexecinfo.so - found
===>   tvheadend-3.4.0.20130726.3_4 depends on shared library: libcurl.so - found
===>  Configuring for tvheadend-3.4.0.20130726.3_4
Checking support/features
  checking for cc execinfo.h ...                    ok
  checking for cc -mmmx ...                         ok
  checking for cc -msse2 ...                        ok
  checking for cc getloadavg ...                    ok
  checking for cc atomic64 ...                      ok
  checking for py module gzip ...                   ok
  checking for bzip2 ...                            ok
  checking for pkg avahi-client  ...                ok
  checking for pkg libavcodec <=55.0.0 ...          fail
  checking for cc sys/inotify.h ...                 fail
  checking for pkg libcurl  ...                     ok

Compiler:
  Using C compiler:                        cc
  Using C flags:                           -O2 -pipe -I/usr/local/include -Wno-conversion -Wno-int-to-pointer-cast -fno-strict-aliasing
  Build for arch:                          amd64

Binaries:
  Using PYTHON:                            /usr/local/bin/python2.7

Options:
  cwc                                      yes
  v4l                                      yes
  linuxdvb                                 yes
  dvbscan                                  no
  timeshift                                yes
  trace                                    yes
  imagecache                               yes
  avahi                                    yes
  zlib                                     no
  libav                                    no
  inotify                                  no
  bundle                                   no
  dvbcsa                                   no
  epoll                                    no
  kqueue                                   yes
  execinfo                                 yes
  mmx                                      yes
  sse2                                     yes
  getloadavg                               yes
  atomic64                                 yes
  py_gzip                                  yes
  bin_bzip2                                yes
  ssl                                      yes

Packages:
  avahi-client                             0.6.31
  libcurl                                  7.34.0

Installation paths:
  Prefix:                                  /usr/local
  Binaries:                                ${prefix}/bin
  Libraries:                               ${prefix}/lib
  Data files:                              ${prefix}/share
  Man pages:                               /usr/local/man

Final Binary:
  /usr/ports/multimedia/tvheadend/work/decke-tvheadend-8a8c1a8/build.freebsd/tvheadend

Tvheadend Data Directory:
  /usr/local/share/tvheadend

===>  Building for tvheadend-3.4.0.20130726.3_4
CC              src/version.o
CC              src/main.o
CC              src/tvhlog.o
CC              src/utils.o
CC              src/wrappers.o
CC              src/access.o
CC              src/dtable.o
CC              src/tcp.o
CC              src/http.o
CC              src/notify.o
CC              src/file.o
CC              src/epg.o
CC              src/epgdb.o
CC              src/epggrab.o
CC              src/spawn.o
CC              src/packet.o
CC              src/streaming.o
CC              src/teletext.o
CC              src/channels.o
CC              src/subscriptions.o
CC              src/service.o
CC              src/psi.o
CC              src/parsers.o
CC              src/parser_h264.o
CC              src/parser_latm.o
CC              src/tsdemux.o
CC              src/bitstream.o
CC              src/htsp_server.o
CC              src/serviceprobe.o
CC              src/htsmsg.o
CC              src/htsmsg_binary.o
CC              src/htsmsg_json.o
CC              src/htsmsg_xml.o
CC              src/misc/dbl.o
CC              src/misc/json.o
CC              src/settings.o
CC              src/htsbuf.o
CC              src/trap.o
CC              src/avg.o
CC              src/htsstr.o
CC              src/rawtsinput.o
CC              src/iptv_input.o
CC              src/avc.o
CC              src/huffman.o
CC              src/filebundle.o
CC              src/config2.o
CC              src/lang_codes.o
CC              src/lang_str.o
CC              src/imagecache.o
CC              src/tvhtime.o
CC              src/tvhpoll.o
CC              src/epggrab/module.o
CC              src/epggrab/channel.o
CC              src/epggrab/module/pyepg.o
CC              src/epggrab/module/xmltv.o
CC              src/plumbing/tsfix.o
CC              src/plumbing/globalheaders.o
CC              src/dvr/dvr_db.o
CC              src/dvr/dvr_rec.o
CC              src/dvr/dvr_autorec.o
CC              src/webui/webui.o
CC              src/webui/comet.o
CC              src/webui/extjs.o
CC              src/webui/simpleui.o
CC              src/webui/statedump.o
CC              src/webui/html.o
CC              src/muxer.o
CC              src/muxer/muxer_pass.o
CC              src/muxer/muxer_tvh.o
CC              src/muxer/tvh/ebml.o
CC              src/muxer/tvh/mkmux.o
CC              src/epggrab/otamux.o
CC              src/epggrab/module/eit.o
CC              src/epggrab/module/opentv.o
CC              src/epggrab/support/freesat_huffman.o
CC              src/timeshift.o
CC              src/timeshift/timeshift_filemgr.o
CC              src/timeshift/timeshift_writer.o
CC              src/timeshift/timeshift_reader.o
CC              src/dvb/dvb.o
CC              src/dvb/dvb_support.o
CC              src/dvb/dvb_charset.o
CC              src/dvb/dvb_fe.o
CC              src/dvb/dvb_tables.o
CC              src/dvb/diseqc.o
CC              src/dvb/dvb_adapter.o
CC              src/dvb/dvb_multiplex.o
CC              src/dvb/dvb_service.o
CC              src/dvb/dvb_preconf.o
CC              src/dvb/dvb_satconf.o
CC              src/dvb/dvb_input_filtered.o
CC              src/dvb/dvb_input_raw.o
CC              src/webui/extjs_dvb.o
CC              src/muxes.o
CC              src/v4l.o
CC              src/webui/extjs_v4l.o
CC              src/avahi.o
CC              src/cwc.o
CC              src/capmt.o
CC              src/ffdecsa/ffdecsa_interface.o
CC              src/ffdecsa/ffdecsa_int.o
CC              src/ffdecsa/ffdecsa_mmx.o
CC              src/ffdecsa/ffdecsa_sse2.o
In file included from src/ffdecsa/ffdecsa_sse2.c:2:
src/ffdecsa/FFdecsa.c: In function 'block_decypher_group':
src/ffdecsa/FFdecsa.c:407: note: use -flax-vector-conversions to permit conversions between vectors with differing element types or numbers of subparts
src/ffdecsa/FFdecsa.c:407: error: incompatible type for argument 1 of '__builtin_ia32_psrlqi128'
src/ffdecsa/FFdecsa.c:407: error: incompatible type for argument 1 of '__builtin_ia32_psrlqi128'
src/ffdecsa/FFdecsa.c:407: error: incompatible type for argument 1 of '__builtin_ia32_psrlqi128'
gmake: *** [/usr/ports/multimedia/tvheadend/work/decke-tvheadend-8a8c1a8/build.freebsd/src/ffdecsa/ffdecsa_sse2.o] Error 1
*** [do-build] Error code 1

Stop in /usr/ports/multimedia/tvheadend.
*** [build] Error code 1

Stop in /usr/ports/multimedia/tvheadend.

Ok, fails as well.

2014-02-07: ada0p2 - ports tree updated via portsnap fetch; portsnap update.

2014-02-06: ada0p2 - ports updated cuse4bsd-kmod and webcamd ports.

2014-02-05: ada0p2 - updated to latest FreeBSD 9.2-stable via make world. dmesg output: normal, verbose.

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.2-STABLE FreeBSD 9.2-STABLE #3 r261516: Wed Feb  5 22:38:36 CET 2014     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

That's it.

2014-02-05: ada0p2 - update source via subversion:

root@kg-f4# svn update /usr/src
[...]
U    /usr/src/bin/chio/chio.c
 U   /usr/src/bin
UU   /usr/src/COPYRIGHT
 U   /usr/src
Updated to revision 261516.

Now check what we have got:

root@kg-f4# egrep "^BRANCH|^REVISION" /usr/src/sys/conf/newvers.sh
REVISION="9.2"
BRANCH="STABLE"

Looks good. Read UPDATING, the upgrade.

2013-01-30: ada0p2 - I unplugged and re-plugged the power on the TerraTec H7. usbconfig now shows it:

root@kg-f4# uname -a
FreeBSD kg-f4.kg4.no 9.1-STABLE FreeBSD 9.1-STABLE #2 r245474: Wed Jan 16 08:15:54 CET 2013     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64
root@kg-f4# usbconfig
ugen0.1: <OHCI root HUB ATI> at usbus0, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen1.1: <EHCI root HUB ATI> at usbus1, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=SAVE
ugen2.1: <OHCI root HUB ATI> at usbus2, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen3.1: <EHCI root HUB ATI> at usbus3, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=SAVE
ugen4.1: <OHCI root HUB ATI> at usbus4, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen5.1: <OHCI root HUB ATI> at usbus5, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen6.1: <EHCI root HUB ATI> at usbus6, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=SAVE
ugen3.3: <PCTV 290e PCTV Systems> at usbus3, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=ON
ugen0.2: <PS2toUSB Adapter GASIA> at usbus0, cfg=0 md=HOST spd=LOW (1.5Mbps) pwr=ON
ugen3.2: <TerraTec H7 TerraTec Electronic GmbH> at usbus3, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=ON

more info on the H7 FreeBSD page.

2013-01-28: ada0p2 - updating ports with portsnap fetch; portsnap update.

2013-01-28: ada0p2 - configuring various things. Enable linux kernel module: adding this to /etc/rc.conf:

# enable linux kernel module
linux_enable="YES"

then doing

root@kg-f4# /etc/rc.d/abi restart
Additional ABI support: linux.

checking with kldstat:

root@kg-f4# kldstat
Id Refs Address            Size     Name
 1    8 0xffffffff80200000 133b2f0  kernel
 2    1 0xffffffff8153c000 3020     amdtemp.ko
 3    1 0xffffffff81612000 1f418    linux.ko

perfect.

2013-01-16: ada0p2 - updated to latest FreeBSD 9.1-stable via subversion, make world. dmesg output: normal, verbose.

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.1-STABLE FreeBSD 9.1-STABLE #2 r245474: Wed Jan 16 08:15:54 CET 2013     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

pciconf output:

tingo@kg-f4$ pciconf -lv
hostb0@pci0:0:0:0:    class=0x060000 card=0x15101849 chip=0x15101022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 14h Processor Root Complex'
    class      = bridge
    subclass   = HOST-PCI
vgapci0@pci0:0:1:0:    class=0x030000 card=0x98021849 chip=0x98021002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'AMD Radeon HD 6310 GraphicsATI'
    class      = display
    subclass   = VGA
hdac0@pci0:0:1:1:    class=0x040300 card=0x13141849 chip=0x13141002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'Wrestler HDMI Audio [Radeon HD 6250/6310]'
    class      = multimedia
    subclass   = HDA
pcib1@pci0:0:4:0:    class=0x060400 card=0x15121849 chip=0x15121022 rev=0x00 hdr=0x01
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 14h Processor Root Port'
    class      = bridge
    subclass   = PCI-PCI
ahci0@pci0:0:17:0:    class=0x010601 card=0x43911849 chip=0x43911002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 SATA Controller [AHCI mode]'
    class      = mass storage
    subclass   = SATA
ohci0@pci0:0:18:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci0@pci0:0:18:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
ohci1@pci0:0:19:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci1@pci0:0:19:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
none0@pci0:0:20:0:    class=0x0c0500 card=0x43851849 chip=0x43851002 rev=0x42 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SBx00 SMBus Controller'
    class      = serial bus
    subclass   = SMBus
atapci0@pci0:0:20:1:    class=0x01018a card=0x439c1849 chip=0x439c1002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 IDE Controller'
    class      = mass storage
    subclass   = ATA
hdac1@pci0:0:20:2:    class=0x040300 card=0x18921849 chip=0x43831002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SBx00 Azalia (Intel HDA)'
    class      = multimedia
    subclass   = HDA
isab0@pci0:0:20:3:    class=0x060100 card=0x439d1849 chip=0x439d1002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 LPC host controller'
    class      = bridge
    subclass   = PCI-ISA
pcib2@pci0:0:20:4:    class=0x060401 card=0x00000000 chip=0x43841002 rev=0x40 hdr=0x01
    vendor     = 'ATI Technologies Inc'
    device     = 'SBx00 PCI to PCI Bridge'
    class      = bridge
    subclass   = PCI-PCI
ohci2@pci0:0:20:5:    class=0x0c0310 card=0x43991849 chip=0x43991002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI2 Controller'
    class      = serial bus
    subclass   = USB
pcib3@pci0:0:21:0:    class=0x060400 card=0x00001002 chip=0x43a01002 rev=0x00 hdr=0x01
    vendor     = 'ATI Technologies Inc'
    device     = 'SB700/SB800 PCI to PCI bridge (PCIE port 0)'
    class      = bridge
    subclass   = PCI-PCI
pcib4@pci0:0:21:1:    class=0x060400 card=0x00001002 chip=0x43a11002 rev=0x00 hdr=0x01
    vendor     = 'ATI Technologies Inc'
    device     = 'SB700/SB800 PCI to PCI bridge (PCIE port 1)'
    class      = bridge
    subclass   = PCI-PCI
ohci3@pci0:0:22:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci2@pci0:0:22:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
hostb1@pci0:0:24:0:    class=0x060000 card=0x00000000 chip=0x17001022 rev=0x43 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 0'
    class      = bridge
    subclass   = HOST-PCI
hostb2@pci0:0:24:1:    class=0x060000 card=0x00000000 chip=0x17011022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 1'
    class      = bridge
    subclass   = HOST-PCI
hostb3@pci0:0:24:2:    class=0x060000 card=0x00000000 chip=0x17021022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 2'
    class      = bridge
    subclass   = HOST-PCI
hostb4@pci0:0:24:3:    class=0x060000 card=0x00000000 chip=0x17031022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 3'
    class      = bridge
    subclass   = HOST-PCI
hostb5@pci0:0:24:4:    class=0x060000 card=0x00000000 chip=0x17041022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 4'
    class      = bridge
    subclass   = HOST-PCI
hostb6@pci0:0:24:5:    class=0x060000 card=0x00000000 chip=0x17181022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 6'
    class      = bridge
    subclass   = HOST-PCI
hostb7@pci0:0:24:6:    class=0x060000 card=0x00000000 chip=0x17161022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 5'
    class      = bridge
    subclass   = HOST-PCI
hostb8@pci0:0:24:7:    class=0x060000 card=0x00000000 chip=0x17191022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 7'
    class      = bridge
    subclass   = HOST-PCI
re0@pci0:4:0:0:    class=0x020000 card=0x81681849 chip=0x816810ec rev=0x06 hdr=0x00
    vendor     = 'Realtek Semiconductor Co., Ltd.'
    device     = 'RTL8111/8168B PCI Express Gigabit Ethernet controller'
    class      = network
    subclass   = ethernet

That is all for now.

2013-01-15: ada0p2 - updating the source via svn:

root@kg-f4# svn co svn://svn.FreeBSD.org/base/stable/9 /usr/src
 :
 U   /usr/src
Checked out revision 245474.

That's it. Verify:

root@kg-f4# egrep "^BRANCH|^REVISION" /usr/src/sys/conf/newvers.sh
REVISION="9.1"
BRANCH="STABLE"

Now update it.

2012-10-13: ada0p2 - updating the ports tree: portsnap fetch

root@kg-f4# portsnap fetch
Looking up portsnap.FreeBSD.org mirrors... 6 mirrors found.
Fetching snapshot tag from ec2-eu-west-1.portsnap.freebsd.org... done.
Fetching snapshot metadata... done.
Updating from Tue Aug 28 17:51:14 CEST 2012 to Sat Oct 13 20:43:44 CEST 2012.
Fetching 4 metadata patches... done.
Applying metadata patches... done.
Fetching 4 metadata files... done.
Fetching 2892 patches.....10....20....30....40....50....60....70....80....90....100....110....120....130....140....150....160....170....180....190....200....210....220....230....240....250....260....270....280....290....300....310....320....330....340....350....360....370....380....390....400....410....420....430....440....450....460....470....480....490....500....510....520....530....540....550....560....570....580....590....600....610....620....630....640....650....660....670....680....690....700....710....720....730....740....750....760....770....780....790....800....810....820....830....840....850....860....870....880....890....900....910....920....930....940....950....960....970....980....990....1000....1010....1020....1030....1040....1050....1060....1070....1080....1090....1100....1110....1120....1130....1140....1150....1160....1170....1180....1190....1200....1210....1220....1230....1240....1250....1260....1270....1280....1290....1300....1310....1320....1330....1340....1350....1360....1370....1380....1390....1400....1410....1420....1430....1440....1450....1460....1470....1480....1490....1500....1510....1520....1530....1540....1550....1560....1570....1580....1590....1600....1610....1620....1630....1640....1650....1660....1670....1680....1690....1700....1710....1720....1730....1740....1750....1760....1770....1780....1790....1800....1810....1820....1830....1840....1850....1860....1870....1880....1890....1900....1910....1920....1930....1940....1950....1960....1970....1980....1990....2000....2010....2020....2030....2040....2050....2060....2070....2080....2090....2100....2110....2120....2130....2140....2150....2160....2170....2180....2190....2200....2210....2220....2230....2240....2250....2260....2270....2280....2290....2300....2310....2320....2330....2340....2350....2360....2370....2380....2390....2400....2410....2420....2430....2440....2450....2460....2470....2480....2490....2500....2510....2520....2530....2540....2550....2560....2570....2580....2590....2600....2610....2620....2630....2640....2650....2660....2670....2680....2690....2700....2710....2720....2730....2740....2750....2760....2770....2780....2790....2800....2810....2820....2830....2840....2850....2860....2870....2880....2890. done.
Applying patches... done.
Fetching 1353 new ports or files... done.

portsnap update

root@kg-f4# portsnap update
(lots of output skipped)
/usr/ports/x11/yeahconsole/
/usr/ports/x11/yelp/
Building new INDEX files... done.

That's it.

2012-10-13: ada0p2 - testing Xorg with the radeon driver again. startx works, but when exiting, the video mode is not correctly restored (the monitor looses signal). From /var/log/xorg.0.log, various info:

Markers: (--) probed, (**) from config file, (==) default setting,
        (++) from command line, (!!) notice, (II) informational,
        (WW) warning, (EE) error, (NI) not implemented, (??) unknown.
(--) PCI:*(0:0:1:0) 1002:9802:1849:9802 Advanced Micro Devices [AMD] nee ATI Wrestler [Radeon HD 6310] rev 0, Mem @ 0xc0000000/268435456, 0xfeb00000/262144, I/O @ 0x0000f000/256, BIOS @ 0x????????/65536
(II) Primary Device is: PCI 00@00:01:0
(WW) VGA arbiter: cannot open kernel arbiter, no multi-card support
(II) RADEON(0): TOTO SAYS 00000000feb00000
(II) RADEON(0): MMIO registers at 0x00000000feb00000: size 256KB
(II) RADEON(0): PCI bus 0 card 1 func 0
(**) RADEON(0): Depth 24, (--) framebuffer bpp 32
(II) RADEON(0): Pixel depth = 24 bits stored in 4 bytes (32 bpp pixmaps)
(==) RADEON(0): Default visual is TrueColor
(==) RADEON(0): RGB weight 888
(II) RADEON(0): Using 8 bits per RGB (8 bit DAC)
(--) RADEON(0): Chipset: "AMD Radeon HD 6310 Graphics" (ChipID = 0x9802)
(--) RADEON(0): Linear framebuffer at 0x00000000c0000000
(II) RADEON(0): PCIE card detected
(II) RADEON(0): ATOM BIOS detected
(II) RADEON(0): ATOM BIOS Rom:
        SubsystemVendorID: 0x1849 SubsystemID: 0x9802
        IOBaseAddress: 0xf000
        Filename: 13C06001.102
        BIOS Bootup Message:
AMD Fusion Wrestler generic VBIOS                                          

(II) RADEON(0): Framebuffer space used by Firmware (kb): 20
(II) RADEON(0): Start of VRAM area used by Firmware: 0x5ffec
(II) RADEON(0): AtomBIOS requests 20kB of VRAM scratch space
(II) RADEON(0): AtomBIOS VRAM scratch base: 0x5ffec
(II) RADEON(0): Cannot get VRAM scratch space. Allocating in main memory instead
(II) RADEON(0): Default Engine Clock: 200000
(II) RADEON(0): Default Memory Clock: 667000
(II) RADEON(0): Maximum Pixel ClockPLL Frequency Output: 1200000
(II) RADEON(0): Minimum Pixel ClockPLL Frequency Output: 0
(II) RADEON(0): Maximum Pixel ClockPLL Frequency Input: 50000
(II) RADEON(0): Minimum Pixel ClockPLL Frequency Input: 6750
(II) RADEON(0): Maximum Pixel Clock: 400000
(II) RADEON(0): Reference Clock: 100000
(II) RADEON(0): No DRI yet on Evergreen
(II) RADEON(0): using shadow framebuffer
(II) RADEON(0): Detected total video RAM=393216K, accessible=262144K (PCI BAR=262144K)
(--) RADEON(0): Mapped VideoRAM: 262144 kByte (128 bit DDR SDRAM)
(II) RADEON(0): EDID data from the display on output: VGA-0 ----------------------
(II) RADEON(0): Manufacturer: BNQ  Model: 7820  Serial#: 21573
(II) RADEON(0): Year: 2009  Week: 8
(II) RADEON(0): EDID Version: 1.3
(II) RADEON(0): Analog Display Input,  Input Voltage Level: 0.700/0.300 V
(II) RADEON(0): Sync:  Separate  Composite  SyncOnGreen
(II) RADEON(0): Max Image Size [cm]: horiz.: 48  vert.: 27
(II) RADEON(0): Gamma: 2.20
(II) RADEON(0): DPMS capabilities: Off; RGB/Color Display
(II) RADEON(0): Default color space is primary color space
(II) RADEON(0): First detailed timing is preferred mode
(II) RADEON(0): redX: 0.648 redY: 0.339   greenX: 0.282 greenY: 0.603
(II) RADEON(0): blueX: 0.143 blueY: 0.070   whiteX: 0.312 whiteY: 0.329
(II) RADEON(0): Supported established timings:
(II) RADEON(0): 720x400@70Hz
(II) RADEON(0): 640x480@60Hz
(II) RADEON(0): 640x480@75Hz
(II) RADEON(0): 800x600@60Hz
(II) RADEON(0): 800x600@75Hz
(II) RADEON(0): 832x624@75Hz
(II) RADEON(0): 1024x768@60Hz
(II) RADEON(0): 1024x768@75Hz
(II) RADEON(0): 1280x1024@75Hz
(II) RADEON(0): 1152x864@75Hz
(II) RADEON(0): Manufacturer's mask: 0
(II) RADEON(0): Supported standard timings:
(II) RADEON(0): #0: hsize: 1152  vsize 720  refresh: 60  vid: 113
(II) RADEON(0): #1: hsize: 1280  vsize 720  refresh: 60  vid: 49281
(II) RADEON(0): #2: hsize: 1280  vsize 960  refresh: 60  vid: 16513
(II) RADEON(0): #3: hsize: 1280  vsize 1024  refresh: 60  vid: 32897
(II) RADEON(0): #4: hsize: 1600  vsize 900  refresh: 60  vid: 49321
(II) RADEON(0): #5: hsize: 1680  vsize 1050  refresh: 60  vid: 179
(II) RADEON(0): #6: hsize: 1920  vsize 1080  refresh: 60  vid: 49361
(II) RADEON(0): Supported detailed timing:
(II) RADEON(0): clock: 148.5 MHz   Image Size:  477 x 268 mm
(II) RADEON(0): h_active: 1920  h_sync: 2008  h_sync_end 2052 h_blank_end 2200 h_border: 0
(II) RADEON(0): v_active: 1080  v_sync: 1084  v_sync_end 1089 v_blanking: 1125 v_border: 0
(II) RADEON(0): Serial No: 72904847SL0
(II) RADEON(0): Ranges: V min: 50 V max: 76 Hz, H min: 24 H max: 83 kHz, PixClock max 170 MHz
(II) RADEON(0): Monitor name: BenQ G2220HD
(II) RADEON(0): Supported established timings:
(II) RADEON(0): 720x400@70Hz
(II) RADEON(0): 640x480@60Hz
(II) RADEON(0): 640x480@75Hz
(II) RADEON(0): 800x600@60Hz
(II) RADEON(0): 800x600@75Hz
(II) RADEON(0): 832x624@75Hz
(II) RADEON(0): 1024x768@60Hz
(II) RADEON(0): 1024x768@75Hz
(II) RADEON(0): 1280x1024@75Hz
(II) RADEON(0): 1152x864@75Hz
(II) RADEON(0): Manufacturer's mask: 0
(II) RADEON(0): Supported standard timings:
(II) RADEON(0): #0: hsize: 1152  vsize 720  refresh: 60  vid: 113
(II) RADEON(0): #1: hsize: 1280  vsize 720  refresh: 60  vid: 49281
(II) RADEON(0): #2: hsize: 1280  vsize 960  refresh: 60  vid: 16513
(II) RADEON(0): #3: hsize: 1280  vsize 1024  refresh: 60  vid: 32897
(II) RADEON(0): #4: hsize: 1600  vsize 900  refresh: 60  vid: 49321
(II) RADEON(0): #5: hsize: 1680  vsize 1050  refresh: 60  vid: 179
(II) RADEON(0): #6: hsize: 1920  vsize 1080  refresh: 60  vid: 49361
(II) RADEON(0): Supported detailed timing:
(II) RADEON(0): clock: 148.5 MHz   Image Size:  477 x 268 mm
(II) RADEON(0): h_active: 1920  h_sync: 2008  h_sync_end 2052 h_blank_end 2200 h_border: 0
(II) RADEON(0): v_active: 1080  v_sync: 1084  v_sync_end 1089 v_blanking: 1125 v_border: 0
(II) RADEON(0): Serial No: 72904847SL0
(II) RADEON(0): Ranges: V min: 50 V max: 76 Hz, H min: 24 H max: 83 kHz, PixClock max 170 MHz
(II) RADEON(0): Monitor name: BenQ G2220HD
(II) RADEON(0): Output VGA-0 connected
(II) RADEON(0): Using exact sizes for initial modes
(II) RADEON(0): Output VGA-0 using initial mode 1920x1080
(II) RADEON(0): Using default gamma of (1.0, 1.0, 1.0) unless otherwise stated.
(==) RADEON(0): DPI set to (96, 96)
(II) RADEON(0): RADEONRestoreMemMapRegisters() :
(II) RADEON(0):   MC_FB_LOCATION   : 0x0f170f00 0x0f170f00
(II) RADEON(0):   MC_AGP_LOCATION  : 0x0003ffff
(==) RADEON(0): Write-combining range (0xa0000,0x10000) was already clear

I don't know if the last few lines indicate an error, or something else.

2012-10-13: ada0p2 - at last, Xfce is installed. I edited /etc/rc.conf, adding:

dbus_enable="YES"

Then it is time to see if we can get Xorg configured. I used Xorg -configure from the console. I moved the resulting xorg.conf.new file to /etc/X11/xorg.conf, and added a few things to it.

Section "ServerLayout", added the line
        Option          "AutoAddDevices" "false"
Section "InputDevice", added the line
        Option      "XkbLayout" "no"
Section "Screen", added the line
        DefaultDepth    24

and the I tested with startx as user root. But that didn't work - all I got was a blank screen. I checked /var/log/Xorg.0.log, but didn't find anything. Let's try with vesa driver instead.

root@kg-f4# cd /etc/X11
root@kg-f4# mv xorg.conf xorg.conf_radeon
root@kg-f4# cp xorg.conf_radeon xorg.conf_vesa

edit the last file to use the vesa driver:

root@kg-f4# diff  xorg.conf_radeon xorg.conf_vesa
118c118
<     Driver      "radeon"
---
>     Driver      "vesa"

link in the vesa file:

root@kg-f4# ln -s xorg.conf_vesa xorg.conf

then reboot the machine and try again. Ok, xterm, twm and xclock is missing (xorg-minimal, remember?) that's the reason why startx fails. Se if installing xterm is enough. Yes, that works. Xorg looks ugly without twm though. And using vesa it comes up in 1280 x 1024 instead of 1920 x 1080. From /var/log/xorg.0.log, various info:

Markers: (--) probed, (**) from config file, (==) default setting,
        (++) from command line, (!!) notice, (II) informational,
        (WW) warning, (EE) error, (NI) not implemented, (??) unknown.
(--) PCI:*(0:0:1:0) 1002:9802:1849:9802 Advanced Micro Devices [AMD] nee ATI Wrestler [Radeon HD 6310] rev 0, Mem @ 0xc0000000/268435456, 0xfeb00000/262144, I/O @ 0x0000f000/256, BIOS @ 0x????????/65536
(II) VESA(0): VESA BIOS detected
(II) VESA(0): VESA VBE Version 3.0
(II) VESA(0): VESA VBE Total Mem: 16384 kB
(II) VESA(0): VESA VBE OEM: AMD ATOMBIOS
(II) VESA(0): VESA VBE OEM Software Rev: 12.36
(II) VESA(0): VESA VBE OEM Vendor: (C) 1988-2010, AMD Technologies Inc.
(II) VESA(0): VESA VBE OEM Product: WRESTLER
(II) VESA(0): VESA VBE OEM Product Rev: 01.00
(II) VESA(0): VESA VBE DDC supported
(II) VESA(0): VESA VBE DDC Level 2
(II) VESA(0): VESA VBE DDC transfer in appr. 1 sec.
(==) VESA(0): Write-combining range (0x0,0x1000) was already clear
(==) VESA(0): Write-combining range (0x0,0x1000) was already clear
(II) VESA(0): VESA VBE DDC read successfully
(II) VESA(0): Manufacturer: BNQ  Model: 7820  Serial#: 21573
(II) VESA(0): Year: 2009  Week: 8
(II) VESA(0): EDID Version: 1.3
(II) VESA(0): Analog Display Input,  Input Voltage Level: 0.700/0.300 V
(II) VESA(0): Sync:  Separate  Composite  SyncOnGreen
(II) VESA(0): Max Image Size [cm]: horiz.: 48  vert.: 27
(II) VESA(0): Gamma: 2.20
(II) VESA(0): DPMS capabilities: Off; RGB/Color Display
(II) VESA(0): Default color space is primary color space
(II) VESA(0): First detailed timing is preferred mode
(II) VESA(0): redX: 0.648 redY: 0.339   greenX: 0.282 greenY: 0.603
(II) VESA(0): blueX: 0.143 blueY: 0.070   whiteX: 0.312 whiteY: 0.329
(II) VESA(0): Supported established timings:
(II) VESA(0): 720x400@70Hz
(II) VESA(0): 640x480@60Hz
(II) VESA(0): 640x480@75Hz
(II) VESA(0): 800x600@60Hz
(II) VESA(0): 800x600@75Hz
(II) VESA(0): 832x624@75Hz
(II) VESA(0): 1024x768@60Hz
(II) VESA(0): 1024x768@75Hz
(II) VESA(0): 1280x1024@75Hz
(II) VESA(0): 1152x864@75Hz
(II) VESA(0): Manufacturer's mask: 0
(II) VESA(0): Supported standard timings:
(II) VESA(0): #0: hsize: 1152  vsize 720  refresh: 60  vid: 113
(II) VESA(0): #1: hsize: 1280  vsize 720  refresh: 60  vid: 49281
(II) VESA(0): #2: hsize: 1280  vsize 960  refresh: 60  vid: 16513
(II) VESA(0): #3: hsize: 1280  vsize 1024  refresh: 60  vid: 32897
(II) VESA(0): #4: hsize: 1600  vsize 900  refresh: 60  vid: 49321
(II) VESA(0): #5: hsize: 1680  vsize 1050  refresh: 60  vid: 179
(II) VESA(0): #6: hsize: 1920  vsize 1080  refresh: 60  vid: 49361
(II) VESA(0): Supported detailed timing:
(II) VESA(0): clock: 148.5 MHz   Image Size:  477 x 268 mm
(II) VESA(0): h_active: 1920  h_sync: 2008  h_sync_end 2052 h_blank_end 2200 h_border: 0
(II) VESA(0): v_active: 1080  v_sync: 1084  v_sync_end 1089 v_blanking: 1125 v_border: 0
(II) VESA(0): Serial No: 72904847SL0
(II) VESA(0): Ranges: V min: 50 V max: 76 Hz, H min: 24 H max: 83 kHz, PixClock max 170 MHz
(II) VESA(0): Monitor name: BenQ G2220HD
(II) VESA(0): Using hsync ranges from config file
(II) VESA(0): Using vrefresh ranges from config file
(II) VESA(0): Printing DDC gathered Modelines:
(II) VESA(0): Modeline "1920x1080"x0.0  148.50  1920 2008 2052 2200  1080 1084 1089 1125 +hsync +vsync (67.5 kHz)
(II) VESA(0): Modeline "800x600"x0.0   40.00  800 840 968 1056  600 601 605 628 +hsync +vsync (37.9 kHz)
(II) VESA(0): Modeline "640x480"x0.0   31.50  640 656 720 840  480 481 484 500 -hsync -vsync (37.5 kHz)
(II) VESA(0): Modeline "640x480"x0.0   25.18  640 656 752 800  480 490 492 525 -hsync -vsync (31.5 kHz)
(II) VESA(0): Modeline "720x400"x0.0   28.32  720 738 846 900  400 412 414 449 -hsync +vsync (31.5 kHz)
(II) VESA(0): Modeline "1280x1024"x0.0  135.00  1280 1296 1440 1688  1024 1025 1028 1066 +hsync +vsync (80.0 kHz)
(II) VESA(0): Modeline "1024x768"x0.0   78.75  1024 1040 1136 1312  768 769 772 800 +hsync +vsync (60.0 kHz)
(II) VESA(0): Modeline "1024x768"x0.0   65.00  1024 1048 1184 1344  768 771 777 806 -hsync -vsync (48.4 kHz)
(II) VESA(0): Modeline "832x624"x0.0   57.28  832 864 928 1152  624 625 628 667 -hsync -vsync (49.7 kHz)
(II) VESA(0): Modeline "800x600"x0.0   49.50  800 816 896 1056  600 601 604 625 +hsync +vsync (46.9 kHz)
(II) VESA(0): Modeline "1152x864"x0.0  108.00  1152 1216 1344 1600  864 865 868 900 +hsync +vsync (67.5 kHz)
(II) VESA(0): Modeline "1152x720"x60.0   67.32  1152 1208 1328 1504  720 721 724 746 -hsync +vsync (44.8 kHz)
(II) VESA(0): Modeline "1280x720"x60.0   74.48  1280 1336 1472 1664  720 721 724 746 -hsync +vsync (44.8 kHz)
(II) VESA(0): Modeline "1280x960"x0.0  108.00  1280 1376 1488 1800  960 961 964 1000 +hsync +vsync (60.0 kHz)
(II) VESA(0): Modeline "1280x1024"x0.0  108.00  1280 1328 1440 1688  1024 1025 1028 1066 +hsync +vsync (64.0 kHz)
(II) VESA(0): Modeline "1600x900"x60.0  119.00  1600 1696 1864 2128  900 901 904 932 -hsync +vsync (55.9 kHz)
(II) VESA(0): Modeline "1680x1050"x0.0  146.25  1680 1784 1960 2240  1050 1053 1059 1089 -hsync +vsync (65.3 kHz)
(II) VESA(0): Modeline "1920x1080"x60.0  172.80  1920 2040 2248 2576  1080 1081 1084 1118 -hsync +vsync (67.1 kHz)
(II) VESA(0): Searching for matching VESA mode(s):
(II) VESA(0): Total Memory: 256 64KB banks (16384kB)
(II) VESA(0): Monitor0: Using hsync range of 24.00-83.00 kHz
(II) VESA(0): Monitor0: Using vrefresh range of 50.00-76.00 Hz
(II) VESA(0): Monitor0: Using maximum pixel clock of 170.00 MHz
(WW) VESA(0): Unable to estimate virtual size
(II) VESA(0): Not using built-in mode "1920x1440" (no mode of this name)
(II) VESA(0): Not using built-in mode "1856x1392" (no mode of this name)
(II) VESA(0): Not using built-in mode "1792x1344" (no mode of this name)
(II) VESA(0): Not using built-in mode "1600x1200" (no mode of this name)
(II) VESA(0): Not using built-in mode "1400x1050" (no mode of this name)
(II) VESA(0): Not using built-in mode "640x350" (no mode of this name)
(II) VESA(0): Not using built-in mode "512x384" (no mode of this name)
(II) VESA(0): Not using built-in mode "320x240" (no mode of this name)
(II) VESA(0): Not using built-in mode "320x200" (no mode of this name)
(--) VESA(0): Virtual size is 1280x1024 (pitch 1280)
(**) VESA(0): *Built-in mode "1280x1024"
(**) VESA(0): *Built-in mode "1280x960"
(**) VESA(0): *Built-in mode "1152x864"
(**) VESA(0): *Built-in mode "1024x768"
(**) VESA(0): *Built-in mode "800x600"
(**) VESA(0): *Built-in mode "640x480"
(**) VESA(0): *Built-in mode "720x400"
(**) VESA(0): Display dimensions: (480, 270) mm
(**) VESA(0): DPI set to (67, 96)
(**) VESA(0): Using "Shadow Framebuffer"
(II) VESA(0): VESA BIOS detected
(II) VESA(0): VESA VBE Version 3.0
(II) VESA(0): VESA VBE Total Mem: 16384 kB
(II) VESA(0): VESA VBE OEM: AMD ATOMBIOS
(II) VESA(0): VESA VBE OEM Software Rev: 12.36
(II) VESA(0): VESA VBE OEM Vendor: (C) 1988-2010, AMD Technologies Inc.
(II) VESA(0): VESA VBE OEM Product: WRESTLER
(II) VESA(0): VESA VBE OEM Product Rev: 01.00
(II) VESA(0): virtual address = 0x804c00000,
        physical address = 0xc0000000, size = 16777216

That's it. startxfce4 as my normal user also works.

2012-10-09: ada0p2 - I installed the xorg-minimal port: portinstall -R xorg-minimal. Checking:

root@kg-f4# portinstall -R xorg-minimal
** Found already installed package(s) of 'x11/xorg-minimal': xorg-minimal-7.5.2

Then I installed xf86-video-ati:

root@kg-f4# pv | grep xf86
libXxf86misc-1.0.3          =  up-to-date with port
libXxf86vm-1.1.1            =  up-to-date with port
xf86-input-keyboard-1.6.1   =  up-to-date with port
xf86-input-mouse-1.7.1      =  up-to-date with port
xf86-video-ati-6.14.3_1     =  up-to-date with port
xf86-video-vesa-2.3.0_2     =  up-to-date with port
xf86bigfontproto-1.2.0      =  up-to-date with port
xf86dgaproto-2.1            =  up-to-date with port
xf86driproto-2.1.1          =  up-to-date with port
xf86miscproto-0.9.3         =  up-to-date with port
xf86vidmodeproto-2.3.1      =  up-to-date with port

Ok, what fonts do we have? None. I installed xorg-fonts, liberation-fonts-ttf,

root@kg-f4# pv | grep font
font-adobe-100dpi-1.0.3     =  up-to-date with port
font-adobe-75dpi-1.0.3      =  up-to-date with port
font-adobe-utopia-100dpi-1.0.4  =  up-to-date with port
font-adobe-utopia-75dpi-1.0.4  =  up-to-date with port
font-adobe-utopia-type1-1.0.4  =  up-to-date with port
font-alias-1.0.3            =  up-to-date with port
font-arabic-misc-1.0.3      =  up-to-date with port
font-bh-100dpi-1.0.3        =  up-to-date with port
font-bh-75dpi-1.0.3         =  up-to-date with port
font-bh-lucidatypewriter-100dpi-1.0.3  =  up-to-date with port
font-bh-lucidatypewriter-75dpi-1.0.3  =  up-to-date with port
font-bh-ttf-1.0.3           =  up-to-date with port
font-bh-type1-1.0.3         =  up-to-date with port
font-bitstream-100dpi-1.0.3  =  up-to-date with port
font-bitstream-75dpi-1.0.3  =  up-to-date with port
font-bitstream-type1-1.0.3  =  up-to-date with port
font-cronyx-cyrillic-1.0.3  =  up-to-date with port
font-cursor-misc-1.0.3      =  up-to-date with port
font-daewoo-misc-1.0.3      =  up-to-date with port
font-dec-misc-1.0.3         =  up-to-date with port
font-ibm-type1-1.0.3        =  up-to-date with port
font-isas-misc-1.0.3        =  up-to-date with port
font-jis-misc-1.0.3         =  up-to-date with port
font-micro-misc-1.0.3       =  up-to-date with port
font-misc-cyrillic-1.0.3    =  up-to-date with port
font-misc-ethiopic-1.0.3    =  up-to-date with port
font-misc-meltho-1.0.3      =  up-to-date with port
font-misc-misc-1.1.2        =  up-to-date with port
font-mutt-misc-1.0.3        =  up-to-date with port
font-schumacher-misc-1.1.2  =  up-to-date with port
font-screen-cyrillic-1.0.4  =  up-to-date with port
font-sony-misc-1.0.3        =  up-to-date with port
font-sun-misc-1.0.3         =  up-to-date with port
font-util-1.2.0             =  up-to-date with port
font-winitzki-cyrillic-1.0.3  =  up-to-date with port
font-xfree86-type1-1.0.4    =  up-to-date with port
fontconfig-2.9.0,1          =  up-to-date with port
fontsproto-2.1.1            =  up-to-date with port
libXfont-1.4.4_1,1          =  up-to-date with port
libfontenc-1.1.0            =  up-to-date with port
mkfontdir-1.0.6             =  up-to-date with port
mkfontscale-1.0.9           =  up-to-date with port
xf86bigfontproto-1.2.0      =  up-to-date with port
xorg-fonts-100dpi-7.5.1     =  up-to-date with port
xorg-fonts-7.5.1            =  up-to-date with port
xorg-fonts-75dpi-7.5.1      =  up-to-date with port
xorg-fonts-cyrillic-7.5.1   =  up-to-date with port
xorg-fonts-miscbitmaps-7.5.1  =  up-to-date with port
xorg-fonts-truetype-7.5.1   =  up-to-date with port
xorg-fonts-type1-7.5.1      =  up-to-date with port

and

root@kg-f4# pv | grep liberation
liberation-fonts-ttf-1.07.0,1  =  up-to-date with port

Next I installed xfce-4.10, taking care to unselect hal in all places.

2012-09-04: ada0p2 - I connected a "scratch" drive to the sata docking adapter, I'm going to use it for storage for Xubuntu and FreeBSD (or compiles etc). The drive looks like this:

root@kg-f4# smartctl -i /dev/da0
smartctl 5.43 2012-06-30 r3573 [FreeBSD 9.1-PRERELEASE amd64] (local build)
Copyright (C) 2002-12 by Bruce Allen, http://smartmontools.sourceforge.net

=== START OF INFORMATION SECTION ===
Model Family:     SAMSUNG SpinPoint M8 (AFT)
Device Model:     SAMSUNG HN-M101MBB
Serial Number:    S2R8J9HB911149
LU WWN Device Id: 5 0024e9 2061ba6c7
Firmware Version: 2AR10001
User Capacity:    1,000,204,886,016 bytes [1.00 TB]
Sector Size:      512 bytes logical/physical
Device is:        In smartctl database [for details use: -P show]
ATA Version is:   8
ATA Standard is:  ATA-8-ACS revision 6
Local Time is:    Tue Sep  4 22:14:12 2012 CEST
SMART support is: Available - device has SMART capability.
SMART support is: Enabled

and has this partition layout now:

root@kg-f4# gpart show -p da0
=>        34  1953525101    da0  GPT  (931G)
          34  1953525101  da0p1  freebsd-ufs  (931G)

Ok, delete that:

root@kg-f4# gpart delete -i 1 da0
da0p1 deleted

Can we create a linux-data partition?

root@kg-f4# gpart add -t linux-data -s 100G da0
da0p1 added
root@kg-f4# gpart show da0
=>        34  1953525101  da0  GPT  (931G)
          34   209715200    1  linux-data  (100G)
   209715234  1743809901       - free -  (831G)

Yes, that worked.

2012-08-31: ada0p2 - create a new GPT on ada1:

root@kg-f4# gpart show ada1
gpart: No such geom: ada1.
nothing there, so create it:
root@kg-f4# gpart create -s GPT ada1
ada1 created
root@kg-f4# gpart show ada1
=>       34  117231341  ada1  GPT  (55G)
         34  117231341        - free -  (55G)

Ok, done here.

2012-08-31: ada0p2 - the new Agility 3 just installed shows up as ada1:

root@kg-f4# camcontrol devlist
<OCZ-AGILITY3 2.22>                at scbus0 target 0 lun 0 (ada0,pass0)
<OCZ-AGILITY3 2.22>                at scbus2 target 0 lun 0 (ada1,pass1)
<HITACHI_ DK23EB-20 A0C0>          at scbus7 target 0 lun 0 (pass2,da0)

From dmesg:

root@kg-f4# dmesg | grep ^ad
ada0 at ahcich0 bus 0 scbus0 target 0 lun 0
ada0: <OCZ-AGILITY3 2.22> ATA-8 SATA 3.x device
ada0: 600.000MB/s transfers (SATA 3.x, UDMA6, PIO 8192bytes)
ada0: Command Queueing enabled
ada0: 57241MB (117231408 512 byte sectors: 16H 63S/T 16383C)
ada0: Previously was known as ad4
ada1 at ahcich2 bus 0 scbus2 target 0 lun 0
ada1: <OCZ-AGILITY3 2.22> ATA-8 SATA 3.x device
ada1: 600.000MB/s transfers (SATA 3.x, UDMA6, PIO 8192bytes)
ada1: Command Queueing enabled
ada1: 57241MB (117231408 512 byte sectors: 16H 63S/T 16383C)
ada1: Previously was known as ad8

Checking firmware with smartctl:

root@kg-f4# smartctl -i /dev/ada1
smartctl 5.43 2012-06-30 r3573 [FreeBSD 9.1-PRERELEASE amd64] (local build)
Copyright (C) 2002-12 by Bruce Allen, http://smartmontools.sourceforge.net

=== START OF INFORMATION SECTION ===
Model Family:     SandForce Driven SSDs
Device Model:     OCZ-AGILITY3
Serial Number:    OCZ-7IU0GE6K2V8E300L
LU WWN Device Id: 5 e83a97 eb55dc01c
Firmware Version: 2.22
User Capacity:    60,022,480,896 bytes [60.0 GB]
Sector Size:      512 bytes logical/physical
Device is:        In smartctl database [for details use: -P show]
ATA Version is:   8
ATA Standard is:  ACS-2 revision 3
Local Time is:    Fri Aug 31 14:26:11 2012 CEST
SMART support is: Available - device has SMART capability.
SMART support is: Enabled

The firmware version is 2.22 - we're good.

2012-08-30: ada0p2 - update webcamd to a newer version:

tingo@kg-f4$ cd ~/work/wcd
tingo@kg-f4$ cd ports
tingo@kg-f4$ svn up
Updating '.':
U    audio/midipp/Makefile
U    audio/midipp/distinfo
U    multimedia/webcamd/Makefile
U    multimedia/webcamd/distinfo
Updated to revision 2417.

Cool. Build the updated version:

tingo@kg-f4$ pwd
/home/tingo/work/wcd/ports
tingo@kg-f4$ cd multimedia/webcamd
tingo@kg-f4$ su
Password:
root@kg-f4# make fetch
===>  License GPLv2 accepted by the user
===>  Found saved configuration for webcamd-3.6.0.1_1
=> webcamd-3.7.0.1.tar.bz2 doesn't seem to exist in /usr/ports/distfiles/.
=> Attempting to fetch ftp://tingo:white12@kg-f2/usr/ports/distfiles//webcamd-3.7.0.1.tar.bz2
fetch: ftp://tingo:white12@kg-f2/usr/ports/distfiles//webcamd-3.7.0.1.tar.bz2: File unavailable (e.g., file not found, no access)
=> Attempting to fetch http://www.selasky.org/hans_petter/distfiles/webcamd-3.7.0.1.tar.bz2
webcamd-3.7.0.1.tar.bz2                       100% of 9243 kB  679 kBps 00m00s
root@kg-f4# exit

tingo@kg-f4$ make

(output skipped)

tingo@kg-f4$ su
Password:

deinstall old version:

root@kg-f4# make deinstall
===>  Deinstalling for multimedia/webcamd
===>   Deinstalling webcamd-3.6.0.2
==> You should manually remove the "webcamd" user.

and install new version:

root@kg-f4# make install
===>  Installing for webcamd-3.7.0.1
===>   webcamd-3.7.0.1 depends on shared library: v4l1.0 - found
===>   webcamd-3.7.0.1 depends on shared library: cuse4bsd.1 - found
===>   Generating temporary packing list
===>  Checking if multimedia/webcamd already installed
===> Creating users and/or groups.
Using existing group `webcamd'.
Using existing user `webcamd'.
install -s -o root -g wheel -m 555   webcamd /usr/local/sbin
install -o root -g wheel -m 444 webcamd.8.gz  /usr/local/man/man8
install -o root -g wheel -m 444 a800.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 af9005.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 af9015.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 anysee.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 au0828.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 au6610.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 b2c2.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 benq.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ce6230.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 cinergy.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 conex.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 cpiax.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 cxusb.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dib0700.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 digitv.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dtt200u.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dtv5100.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dw2102.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ec168.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 em28xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 et61x251.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 finepix.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 friio.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 gl860.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 gl861.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 gp8psk.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 hdpvr.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ibmcam.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 jeilinj.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 m5602.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 m920x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 mars.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 mr800.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 mr97310a.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 nova-t.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 opera.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ov519.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ov534.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 pacxxx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 pvrusb2.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 pwc.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 s2255.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 se401.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 siano.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sn9c102.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sn9c20x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sonixj.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 spca5xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sq905c.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 stk014.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 stv06xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sunplus.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 t613.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ttusb2.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 tv8532.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 umt.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 usbvision.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 uvc.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 vc032x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 vp702x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 vp7045.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 zc3xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 zr364xx.4.gz  /usr/local/man/man4
===> Installing rc.d startup script(s)
install  -o root -g wheel -m 444 "/usr/home/tingo/work/wcd/ports/multimedia/webcamd/work/webcamd.conf" /usr/local/etc/devd
*********************************************************************
1) webcamd requires the cuse4bsd kernel module, please load this
by doing

       # kldload cuse4bsd

or adding

       cuse4bsd_load="YES"

to your /boot/loader.conf.

2) Please restart devd as the configuration changed

    # /etc/rc.d/devd restart

*********************************************************************
===> Correct pkg-plist sequence to create group(s) and user(s)
===>   Running ldconfig
/sbin/ldconfig -m /usr/local/lib
===>   Registering installation for webcamd-3.7.0.1

That is all.

2012-08-30: ada0p2 - ok, it helps if the TerraTec H7 has external power (classic user error there!):

root@kg-f4# usbconfig
ugen0.1: <OHCI root HUB ATI> at usbus0, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen1.1: <EHCI root HUB ATI> at usbus1, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=SAVE
ugen2.1: <OHCI root HUB ATI> at usbus2, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen3.1: <EHCI root HUB ATI> at usbus3, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=SAVE
ugen4.1: <OHCI root HUB ATI> at usbus4, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen5.1: <OHCI root HUB ATI> at usbus5, cfg=0 md=HOST spd=FULL (12Mbps) pwr=SAVE
ugen6.1: <EHCI root HUB ATI> at usbus6, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=SAVE
ugen0.2: <PS2 to USB Converter CHESEN> at usbus0, cfg=0 md=HOST spd=LOW (1.5Mbps) pwr=ON
ugen1.3: <PCTV 290e PCTV Systems> at usbus1, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=ON
ugen1.4: <USB to ATAATAPI Bridge JMicron> at usbus1, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=ON
ugen1.2: <TerraTec H7 TerraTec Electronic GmbH> at usbus1, cfg=0 md=HOST spd=HIGH (480Mbps) pwr=ON

That's all.

2012-08-30: ada0p2 - I connected the external drive which has linux (Xubuntu 11.10 on it), It shows up as da1:

root@kg-f4# camcontrol devlist
<OCZ-AGILITY3 2.22>                at scbus0 target 0 lun 0 (ada0,pass0)
<Generic External 1.04>            at scbus7 target 0 lun 0 (da0,pass1)
<HITACHI_ DK23EB-20 A0C0>          at scbus8 target 0 lun 0 (pass2,da1)
gpart shows it like this:
root@kg-f4# gpart show da1
=>      63  39070017  da1  MBR  (18G)
        63      1985       - free -  (992k)
      2048  23083008    1  linux-data  [active]  (11G)
  23085056      2046       - free -  (1M)
  23087102  15982594    2  ebr  (7.6G)
  39069696       384       - free -  (192k)

root@kg-f4# gpart show da1s2
=>       0  15982594  da1s2  EBR  (7.6G)
         0  15982594      1  linux-swap  (7.6G)

That's it.

2012-08-29: ada0p2 - compiling a newer version of webcamd:

tingo@kg-f4$ pwd
/home/tingo/work/wcd/ports/multimedia/webcamd
tingo@kg-f4$ make

(lots of output snipped) install it:

tingo@kg-f4$ su
root@kg-f4# make install
===>  Installing for webcamd-3.6.0.2
===>   webcamd-3.6.0.2 depends on shared library: v4l1.0 - found
===>   webcamd-3.6.0.2 depends on shared library: cuse4bsd.1 - found
===>   Generating temporary packing list
===>  Checking if multimedia/webcamd already installed
===> Creating users and/or groups.
Using existing group `webcamd'.
Using existing user `webcamd'.
install -s -o root -g wheel -m 555   webcamd /usr/local/sbin
install -o root -g wheel -m 444 webcamd.8.gz  /usr/local/man/man8
install -o root -g wheel -m 444 a800.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 af9005.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 af9015.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 anysee.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 au0828.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 au6610.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 b2c2.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 benq.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ce6230.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 cinergy.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 conex.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 cpiax.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 cxusb.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dib0700.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 digitv.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dtt200u.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dtv5100.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 dw2102.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ec168.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 em28xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 et61x251.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 finepix.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 friio.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 gl860.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 gl861.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 gp8psk.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 hdpvr.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ibmcam.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 jeilinj.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 m5602.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 m920x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 mars.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 mr800.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 mr97310a.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 nova-t.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 opera.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ov519.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ov534.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 pacxxx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 pvrusb2.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 pwc.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 s2255.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 se401.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 siano.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sn9c102.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sn9c20x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sonixj.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 spca5xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sq905c.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 stk014.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 stv06xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 sunplus.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 t613.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 ttusb2.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 tv8532.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 umt.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 usbvision.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 uvc.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 vc032x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 vp702x.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 vp7045.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 zc3xx.4.gz  /usr/local/man/man4
install -o root -g wheel -m 444 zr364xx.4.gz  /usr/local/man/man4
===> Installing rc.d startup script(s)
install  -o root -g wheel -m 444 "/usr/home/tingo/work/wcd/ports/multimedia/webcamd/work/webcamd.conf" /usr/local/etc/devd
*********************************************************************
1) webcamd requires the cuse4bsd kernel module, please load this
by doing

       # kldload cuse4bsd

or adding

       cuse4bsd_load="YES"

to your /boot/loader.conf.

2) Please restart devd as the configuration changed

    # /etc/rc.d/devd restart

*********************************************************************
===> Correct pkg-plist sequence to create group(s) and user(s)
===>   Running ldconfig
/sbin/ldconfig -m /usr/local/lib
===>   Registering installation for webcamd-3.6.0.2
root@kg-f4#

Done.

2012-08-29: ada0p2 - getting a newer version of webcamd:

mkdir -p work/wcd
cd work/wcd

tingo@kg-f4$ svn --username anonsvn --password anonsvn checkout svn://svn.turbocat.net/i4b/trunk/ports

-----------------------------------------------------------------------
ATTENTION!  Your password for authentication realm:

   <svn://svn.turbocat.net:3690> 4429bdba-5c01-0410-9f4f-ee3375ed255f

can only be stored to disk unencrypted!  You are advised to configure
your system so that Subversion can store passwords encrypted, if
possible.  See the documentation for details.

You can avoid future appearances of this warning by setting the value
of the 'store-plaintext-passwords' option to either 'yes' or 'no' in
'/home/tingo/.subversion/servers'.
-----------------------------------------------------------------------
Store password unencrypted (yes/no)? yes
A    ports/audio
A    ports/audio/jack-keyboard
A    ports/audio/jack-keyboard/pkg-plist
A    ports/audio/jack-keyboard/Makefile
A    ports/audio/jack-keyboard/distinfo
A    ports/audio/jack-keyboard/pkg-descr
A    ports/audio/jack_ghero
A    ports/audio/jack_ghero/Makefile
A    ports/audio/jack_ghero/distinfo
A    ports/audio/jack_ghero/pkg-descr
A    ports/audio/Makefile
A    ports/audio/libumidi
A    ports/audio/libumidi/distinfo
A    ports/audio/libumidi/pkg-descr
A    ports/audio/libumidi/pkg-plist
A    ports/audio/libumidi/Makefile
A    ports/audio/jack_umidi
A    ports/audio/jack_umidi/Makefile
A    ports/audio/jack_umidi/distinfo
A    ports/audio/jack_umidi/pkg-descr
A    ports/audio/midipp
A    ports/audio/midipp/pkg-plist
A    ports/audio/midipp/Makefile
A    ports/audio/midipp/distinfo
A    ports/audio/midipp/pkg-descr
A    ports/multimedia
A    ports/multimedia/Makefile
A    ports/multimedia/webcamd
A    ports/multimedia/webcamd/pkg-plist
A    ports/multimedia/webcamd/Makefile
A    ports/multimedia/webcamd/distinfo
A    ports/multimedia/webcamd/pkg-descr
A    ports/multimedia/webcamd/files
A    ports/multimedia/webcamd/files/webcamd.in
A    ports/multimedia/webcamd/files/webcamd.conf.in
A    ports/multimedia/webcamd/pkg-message
A    ports/multimedia/cuse4bsd-kmod
A    ports/multimedia/cuse4bsd-kmod/pkg-plist
A    ports/multimedia/cuse4bsd-kmod/Makefile
A    ports/multimedia/cuse4bsd-kmod/distinfo
A    ports/multimedia/cuse4bsd-kmod/pkg-descr
A    ports/Makefile
A    ports/comms
A    ports/comms/isdn4bsd-utils
A    ports/comms/isdn4bsd-utils/Makefile
A    ports/comms/isdn4bsd-utils/distinfo
A    ports/comms/isdn4bsd-utils/pkg-descr
A    ports/comms/Makefile
A    ports/comms/isdn4bsd-kmod
A    ports/comms/isdn4bsd-kmod/pkg-plist
A    ports/comms/isdn4bsd-kmod/Makefile
A    ports/comms/isdn4bsd-kmod/distinfo
A    ports/comms/isdn4bsd-kmod/pkg-descr
A    ports/comms/isdn4bsd-headers
A    ports/comms/libcapi
A    ports/comms/libcapi/Makefile
A    ports/comms/libcapi/distinfo
A    ports/comms/libcapi/pkg-descr
A    ports/comms/chan_capi
A    ports/comms/chan_capi/pkg-plist
A    ports/comms/chan_capi/Makefile
A    ports/comms/chan_capi/distinfo
A    ports/comms/chan_capi/pkg-descr
Checked out revision 2406.

Cool.

2012-08-29: ada0p2 - installing subversion (needed for testing a new webcamd port):

root@kg-f4# portinstall -R subversion-1.7.5

(lots of output) done. Install multimedia/w_scan in order to test a dvb device:

root@kg-f4# portinstall -R w_scan

(lots of output) done.

2012-08-28: ada0p2 - getting a ports tree onto the machine:

root@kg-f4# portsnap fetch
Looking up portsnap.FreeBSD.org mirrors... 9 mirrors found.
Fetching public key from geodns-1.portsnap.freebsd.org... done.
Fetching snapshot tag from geodns-1.portsnap.freebsd.org... done.
Fetching snapshot metadata... done.
Fetching snapshot generated at Tue Aug 28 02:03:14 CEST 2012:
2ebdc8e8dea96c9a625ff06ff5687e82f18e673a183814100% of   67 MB 2706 kBps 00m00s
Extracting snapshot... done.
Verifying snapshot integrity... done.
Fetching snapshot tag from geodns-1.portsnap.freebsd.org... done.
Fetching snapshot metadata... done.
Updating from Tue Aug 28 02:03:14 CEST 2012 to Tue Aug 28 17:51:14 CEST 2012.
Fetching 4 metadata patches... done.
Applying metadata patches... done.
Fetching 0 metadata files... done.
Fetching 21 patches.....10....20 done.
Applying patches... done.
Fetching 3 new ports or files... done.

and unpack it:

root@kg-f4# portsnap extract

(lots of output)

/usr/ports/x11/zenity/
Building new INDEX files... done.

Ok, no ready to install ports. smartmontools first:

root@kg-f4# cd /usr/ports/sysutils/smartmontools

(fixing an /etc/make.conf file first)

make
make install
make clean

That is all.

2012-08-05: da0s1a - booted FreeBSD 8.2-stable from external drive, in order to test amdtemp patch:

root@kg-f4# uname -a
FreeBSD kg-f4.kg4.no 8.2-STABLE FreeBSD 8.2-STABLE #0: Sat Nov  5 01:54:44 CET 2011     root@kg-f3.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64
root@kg-f4# df -h
Filesystem     Size    Used   Avail Capacity  Mounted on
/dev/da0s1a    841M    125M    648M    16%    /
devfs          1.0k    1.0k      0B   100%    /dev
/dev/da0s1e    726M    188k    667M     0%    /tmp
/dev/da0s1f    6.2G    3.3G    2.4G    58%    /usr
/dev/da0s1d    2.9G    130M    2.5G     5%    /var
testing the amdtemp module:
```sh
root@kg-f4# kldload amdtemp
root@kg-f4# dmesg | grep amdtemp
root@kg-f4# sysctl dev.amdtemp
sysctl: unknown oid 'dev.amdtemp'

ok, test the patch from PR kern/156358 does it work?

root@kg-f4# cd /usr/src/sys/dev/amdtemp
root@kg-f4# patch -C -p3 < /home/tingo/dl/amdtemp_fusion_8.x.diff
Hmm...  Looks like a unified diff to me...
The text leading up to this was:
--------------------------
|--- sys/dev/amdtemp/amdtemp.c.orig      2009-08-20 21:23:28.000000000 +0100
|+++ sys/dev/amdtemp/amdtemp.c   2011-04-11 15:01:11.000000000 +0100
--------------------------
Patching file amdtemp.c using Plan A...
Hunk #1 failed at 72.
Hunk #2 failed at 81.
2 out of 2 hunks failed--saving rejects to amdtemp.c.rej
done

Nope. Ok, apply manually then. Next, build a new kernel. After kernel build, load the amdtemp module and test. does it work?

root@kg-f4# kldload amdtemp
root@kg-f4# dmesg | grep amdtemp
amdtemp0: <AMD K8 Thermal Sensors> on hostb4
root@kg-f4# sysctl dev.amdtemp
dev.amdtemp.0.%desc: AMD K8 Thermal Sensors
dev.amdtemp.0.%driver: amdtemp
dev.amdtemp.0.%parent: hostb4

Well, it is detected, but no sensors. Ok, the sensors are here:

root@kg-f4# sysctl dev.cpu.0.temperature;sysctl dev.cpu.1.temperature
dev.cpu.0.temperature: 56.5C
dev.cpu.1.temperature: 56.5C

Cool!.

2012-08-05: ada0p2 - upgraded to FreeBSD 9.1-prerelease, using csup and make world. dmesg output: normal, verbose.

root@kg-f4# uname -a
FreeBSD kg-f4.kg4.no 9.1-PRERELEASE FreeBSD 9.1-PRERELEASE #0: Sun Aug  5 13:17:07 CEST 2012     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64
root@kg-f4# df -h
Filesystem     Size    Used   Avail Capacity  Mounted on
/dev/ada0p2     25G    4.3G     18G    19%    /
devfs          1.0k    1.0k      0B   100%    /dev
root@kg-f4# swapinfo
Device          1K-blocks     Used    Avail Capacity
/dev/ada0p3       4194304        0  4194304     0%

Just verifying that the amdtemp module doesn't work:

root@kg-f4# kldstat
Id Refs Address            Size     Name
 1    3 0xffffffff80200000 1320ec0  kernel
 2    1 0xffffffff81521000 3028     amdtemp.ko
root@kg-f4# sysctl dev.amdtemp
sysctl: unknown oid 'dev.amdtemp'

Now, let's try to patch it:

root@kg-f4# cd /usr/src/sys/dev/amdtemp
root@kg-f4# patch -C < /home/tingo/dl/amdtemp_fusion_test.diff
Hmm...  Looks like a unified diff to me...
The text leading up to this was:
--------------------------
|--- amdtemp.c-orij    2011-11-22 14:01:44.000000000 +0900
|+++ amdtemp.c    2011-11-22 14:06:16.000000000 +0900
--------------------------
Patching file amdtemp.c using Plan A...
Hunk #1 succeeded at 76.
Hunk #2 succeeded at 85.
Hunk #3 succeeded at 192.
Hunk #4 succeeded at 285.
done

Ok, dry run worked, now patch for real:

root@kg-f4# patch  < /home/tingo/dl/amdtemp_fusion_test.diff
Hmm...  Looks like a unified diff to me...
The text leading up to this was:
--------------------------
|--- amdtemp.c-orij    2011-11-22 14:01:44.000000000 +0900
|+++ amdtemp.c    2011-11-22 14:06:16.000000000 +0900
--------------------------
Patching file amdtemp.c using Plan A...
Hunk #1 succeeded at 76.
Hunk #2 succeeded at 85.
Hunk #3 succeeded at 192.
Hunk #4 succeeded at 285.
done

and build a new kernel:

root@kg-f4# cd /usr/src
root@kg-f4# make kernel

then reboot and test:

root@kg-f4# uname -a
FreeBSD kg-f4.kg4.no 9.1-PRERELEASE FreeBSD 9.1-PRERELEASE #1: Sun Aug  5 18:43:08 CEST 2012     root@kg-f4.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64
root@kg-f4# kldstat
Id Refs Address            Size     Name
 1    3 0xffffffff80200000 1320ec0  kernel
 2    1 0xffffffff81521000 3048     amdtemp.ko
root@kg-f4# dmesg | grep amdtemp
amdtemp0: <AMD CPU On-Die Thermal Sensors> on hostb4
root@kg-f4# sysctl dev.amdtemp
dev.amdtemp.0.%desc: AMD CPU On-Die Thermal Sensors
dev.amdtemp.0.%driver: amdtemp
dev.amdtemp.0.%parent: hostb4
dev.amdtemp.0.sensor0.core0: 55.5C

Yes, it works.

2012-08-04: ada0p2 - but the amdtemp module doesn't work here:

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.1-BETA1 FreeBSD 9.1-BETA1 #0: Thu Jul 12 09:38:51 UTC 2012     root@farrell.cse.buffalo.edu:/usr/obj/usr/src/sys/GENERIC  amd64
tingo@kg-f4$ df -h
Filesystem     Size    Used   Avail Capacity  Mounted on
/dev/ada0p2     25G    703M     22G     3%    /
devfs          1.0k    1.0k      0B   100%    /dev
tingo@kg-f4$ kldstat
Id Refs Address            Size     Name
 1    3 0xffffffff80200000 1320928  kernel
 2    1 0xffffffff81521000 3020     amdtemp.ko
tingo@kg-f4$ sysctl dev.amdtemp
sysctl: unknown oid 'dev.amdtemp'

Aha, it seems I need a patch (found here). Ok, prepare to install sources:

root@kg-f4# mkdir -p /usr/local/etc/cvsup
root@kg-f4# cp /usr/share/examples/cvsup/stable-supfile /usr/local/etc/cvsup/fbsd9
root@kg-f4# chmod u+w /usr/local/etc/cvsup/fbsd9

Edit the file, to set cvsup server. Then use csup to update sources:

root@kg-f4# csup /usr/local/etc/cvsup/fbsd9

Next, it is patch and make world time.

2012-08-04: da0s2a - interesting, the amdtemp module works here:

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.0-RC1 FreeBSD 9.0-RC1 #0: Thu Nov 24 22:48:50 CET 2011     root@kg-f3.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64
tingo@kg-f4$ df -h
Filesystem     Size    Used   Avail Capacity  Mounted on
/dev/da0s2a     12G    4.2G    7.6G    35%    /
devfs          1.0k    1.0k      0B   100%    /dev
tingo@kg-f4$ gpart show da0
=>       63  117210177  da0  MBR  (55G)
         63   29350692    1  freebsd  (14G)
   29350755   29360079    2  freebsd  [active]  (14G)
   58710834   58499406       - free -  (27G)
tingo@kg-f4$ kldstat
Id Refs Address            Size     Name
 1    3 0xffffffff80200000 11d3e90  kernel
 2    1 0xffffffff813d4000 3040     amdtemp.ko
tingo@kg-f4$ sysctl dev.amdtemp
dev.amdtemp.0.%desc: AMD CPU On-Die Thermal Sensors
dev.amdtemp.0.%driver: amdtemp
dev.amdtemp.0.%parent: hostb4
dev.amdtemp.0.sensor0.core0: 55.5C

2012-08-04: ada0p2 - FreeBSD 9.1-beta1 installed. dmesg output: normal, verbose.

root@kg-f4:/root # uname -a
FreeBSD kg-f4.kg4.no 9.1-BETA1 FreeBSD 9.1-BETA1 #0: Thu Jul 12 09:38:51 UTC 2012     root@farrell.cse.buffalo.edu:/usr/obj/usr/src/sys/GENERIC  amd64
root@kg-f4:/root # df -h
Filesystem     Size    Used   Avail Capacity  Mounted on
/dev/ada0p2     25G    703M     22G     3%    /
devfs          1.0k    1.0k      0B   100%    /dev

2012-08-04: preparing to install FreeBSD 9.1-beta1 onto the internal SSD drive, by writing the image to a usb stick:

root@kg-v2# dd if=./FreeBSD-9.1-BETA1-amd64-memstick.img of=/dev/da1 bs=10240 conv=sync
69694+1 records in
69695+0 records out
713676800 bytes transferred in 359.900602 secs (1982983 bytes/sec)

Now to install it. Installation was easy, I used manual partitioning, in order to split the SSD in two. After the installation, I started a shell and fixed /etc/dhclient.conf so that my machine would get the correct ip address. Nice! I also opted to not install a user account from within the install program, I just used sysinstall to do that afterwards, that way I could set up my favorite group ("users") first. Cool!

2012-08-04: da0s2a - after upgrade of the SSD firmware, dmesg reports:

root@kg-f4# dmesg | grep ada
ada0 at ahcich0 bus 0 scbus0 target 0 lun 0
ada0: <OCZ-AGILITY3 2.22> ATA-8 SATA 3.x device
ada0: 600.000MB/s transfers (SATA 3.x, UDMA6, PIO 8192bytes)
ada0: Command Queueing enabled
ada0: 57241MB (117231408 512 byte sectors: 16H 63S/T 16383C)
ada0: Previously was known as ad4

smartctl reports:

root@kg-f4# smartctl -a /dev/ada0 | more
smartctl 5.41 2011-06-09 r3365 [FreeBSD 9.0-RC1 amd64] (local build)
Copyright (C) 2002-11 by Bruce Allen, http://smartmontools.sourceforge.net

=== START OF INFORMATION SECTION ===
Device Model:     OCZ-AGILITY3
Serial Number:    OCZ-1836ZAD2Y6V465NW
LU WWN Device Id: 5 e83a97 fb523c64d
Firmware Version: 2.22
User Capacity:    60,022,480,896 bytes [60.0 GB]
Sector Size:      512 bytes logical/physical
Device is:        Not in smartctl database [for details use: -P showall]
ATA Version is:   8
ATA Standard is:  ACS-2 revision 3
Local Time is:    Sat Aug  4 21:13:45 2012 CEST
SMART support is: Available - device has SMART capability.
SMART support is: Enabled

Nice.

2012-08-04: da0s2a - with the SSD connected, dmesg reports:

root@kg-f4# dmesg | grep ada
ada0 at ahcich0 bus 0 scbus0 target 0 lun 0
ada0: <OCZ-AGILITY3 2.11> ATA-8 SATA 3.x device
ada0: 600.000MB/s transfers (SATA 3.x, UDMA6, PIO 8192bytes)
ada0: Command Queueing enabled
ada0: 57241MB (117231408 512 byte sectors: 16H 63S/T 16383C)
ada0: Previously was known as ad4

and smartctl says:

root@kg-f4# smartctl -a /dev/ada0
smartctl 5.41 2011-06-09 r3365 [FreeBSD 9.0-RC1 amd64] (local build)
Copyright (C) 2002-11 by Bruce Allen, http://smartmontools.sourceforge.net

=== START OF INFORMATION SECTION ===
Device Model:     OCZ-AGILITY3
Serial Number:    OCZ-1836ZAD2Y6V465NW
LU WWN Device Id: 5 e83a97 fb523c64d
Firmware Version: 2.11
User Capacity:    60,022,480,896 bytes [60.0 GB]
Sector Size:      512 bytes logical/physical
Device is:        Not in smartctl database [for details use: -P showall]
ATA Version is:   8
ATA Standard is:  ACS-2 revision 3
Local Time is:    Sat Aug  4 20:27:03 2012 CEST
SMART support is: Available - device has SMART capability.
SMART support is: Disabled

SMART Disabled. Use option -s with argument 'on' to enable it.

So, the SSD firmware is 2.11 which is newer than 2.08, so I'm all set.

2012-08-04: da0s2a - I booted, it stopped at the mountroot prompt, I had to input ufs:/dev/da0s2a manually. after that machine had finished booting, I fixed /etc/fstab (changing da1 into da0, this drive had been used with another machine). Still runs 9.0-RC1:

root@kg-f4# uname -a
FreeBSD kg-f4.kg4.no 9.0-RC1 FreeBSD 9.0-RC1 #0: Thu Nov 24 22:48:50 CET 2011     root@kg-f3.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

That's it.

2012-01-28: da0s2 - I booted FreeBSD 9.0-RC1. dmesg output: normal, verbose.

tingo@kg-f4$ uname -a
FreeBSD kg-f4.kg4.no 9.0-RC1 FreeBSD 9.0-RC1 #0: Thu Nov 24 22:48:50 CET 2011     root@kg-f3.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

pciconf -lv output:

root@kg-f4# pciconf -lv
hostb0@pci0:0:0:0:    class=0x060000 card=0x15101849 chip=0x15101022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 14h Processor Root Complex'
    class      = bridge
    subclass   = HOST-PCI
vgapci0@pci0:0:1:0:    class=0x030000 card=0x98021849 chip=0x98021002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'AMD Radeon HD 6310 GraphicsATI'
    class      = display
    subclass   = VGA
hdac0@pci0:0:1:1:    class=0x040300 card=0x13141849 chip=0x13141002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'Wrestler HDMI Audio [Radeon HD 6250/6310]'
    class      = multimedia
    subclass   = HDA
pcib1@pci0:0:4:0:    class=0x060400 card=0x12341022 chip=0x15121022 rev=0x00 hdr=0x01
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 14h Processor Root Port'
    class      = bridge
    subclass   = PCI-PCI
ahci0@pci0:0:17:0:    class=0x01018f card=0x43901849 chip=0x43901002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 SATA Controller [IDE mode]'
    class      = mass storage
    subclass   = ATA
ohci0@pci0:0:18:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci0@pci0:0:18:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
ohci1@pci0:0:19:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci1@pci0:0:19:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
none0@pci0:0:20:0:    class=0x0c0500 card=0x43851849 chip=0x43851002 rev=0x42 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SBx00 SMBus Controller'
    class      = serial bus
    subclass   = SMBus
atapci0@pci0:0:20:1:    class=0x01018a card=0x439c1849 chip=0x439c1002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 IDE Controller'
    class      = mass storage
    subclass   = ATA
hdac1@pci0:0:20:2:    class=0x040300 card=0x18921849 chip=0x43831002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SBx00 Azalia (Intel HDA)'
    class      = multimedia
    subclass   = HDA
isab0@pci0:0:20:3:    class=0x060100 card=0x439d1849 chip=0x439d1002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 LPC host controller'
    class      = bridge
    subclass   = PCI-ISA
pcib2@pci0:0:20:4:    class=0x060401 card=0x00000000 chip=0x43841002 rev=0x40 hdr=0x01
    vendor     = 'ATI Technologies Inc'
    device     = 'SBx00 PCI to PCI Bridge'
    class      = bridge
    subclass   = PCI-PCI
ohci2@pci0:0:20:5:    class=0x0c0310 card=0x43991849 chip=0x43991002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI2 Controller'
    class      = serial bus
    subclass   = USB
pcib3@pci0:0:21:0:    class=0x060400 card=0x00001002 chip=0x43a01002 rev=0x00 hdr=0x01
    vendor     = 'ATI Technologies Inc'
    device     = 'SB700/SB800 PCI to PCI bridge (PCIE port 0)'
    class      = bridge
    subclass   = PCI-PCI
pcib4@pci0:0:21:1:    class=0x060400 card=0x00001002 chip=0x43a11002 rev=0x00 hdr=0x01
    vendor     = 'ATI Technologies Inc'
    device     = 'SB700/SB800 PCI to PCI bridge (PCIE port 1)'
    class      = bridge
    subclass   = PCI-PCI
ohci3@pci0:0:22:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci2@pci0:0:22:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc'
    device     = 'SB7x0/SB8x0/SB9x0 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
hostb1@pci0:0:24:0:    class=0x060000 card=0x00000000 chip=0x17001022 rev=0x43 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 0'
    class      = bridge
    subclass   = HOST-PCI
hostb2@pci0:0:24:1:    class=0x060000 card=0x00000000 chip=0x17011022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 1'
    class      = bridge
    subclass   = HOST-PCI
hostb3@pci0:0:24:2:    class=0x060000 card=0x00000000 chip=0x17021022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 2'
    class      = bridge
    subclass   = HOST-PCI
hostb4@pci0:0:24:3:    class=0x060000 card=0x00000000 chip=0x17031022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 3'
    class      = bridge
    subclass   = HOST-PCI
hostb5@pci0:0:24:4:    class=0x060000 card=0x00000000 chip=0x17041022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 4'
    class      = bridge
    subclass   = HOST-PCI
hostb6@pci0:0:24:5:    class=0x060000 card=0x00000000 chip=0x17181022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 6'
    class      = bridge
    subclass   = HOST-PCI
hostb7@pci0:0:24:6:    class=0x060000 card=0x00000000 chip=0x17161022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 5'
    class      = bridge
    subclass   = HOST-PCI
hostb8@pci0:0:24:7:    class=0x060000 card=0x00000000 chip=0x17191022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices [AMD]'
    device     = 'Family 12h/14h Processor Function 7'
    class      = bridge
    subclass   = HOST-PCI
re0@pci0:4:0:0:    class=0x020000 card=0x81681849 chip=0x816810ec rev=0x06 hdr=0x00
    vendor     = 'Realtek Semiconductor Co., Ltd.'
    device     = 'RTL8111/8168B PCI Express Gigabit Ethernet controller'
    class      = network
    subclass   = ethernet

temperature monitoring through amdtemp:

root@kg-f4# sysctl dev.amdtemp
dev.amdtemp.0.%desc: AMD CPU On-Die Thermal Sensors
dev.amdtemp.0.%driver: amdtemp
dev.amdtemp.0.%parent: hostb4
dev.amdtemp.0.sensor0.core0: 60.0C
root@kg-f4# sysctl dev.cpu.0.temperature
dev.cpu.0.temperature: 60.0C
root@kg-f4# sysctl dev.cpu.1.temperature
dev.cpu.1.temperature: 60.0C

That's it.

2012-01-28: da0s1 - FreeBSD 8.2-stable.I booted from this drive (previously used to test the f3 machine), and corrected /etc/dhclient.conf and /etc/rc.conf, then rebooted. dmesg output: normal, verbose. I mounted /dev/da0s2a on /mnt and corrected /mnt/etc/dhclient.conf and /mnt/etc/rc.conf there as well.

root@kg-f4# uname -a
FreeBSD kg-f4.kg4.no 8.2-STABLE FreeBSD 8.2-STABLE #0: Sat Nov  5 01:54:44 CET 2011     root@kg-f3.kg4.no:/usr/obj/usr/src/sys/GENERIC  amd64

output from pciconf -lv:

root@kg-f4# pciconf -lv
hostb0@pci0:0:0:0:    class=0x060000 card=0x15101849 chip=0x15101022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
vgapci0@pci0:0:1:0:    class=0x030000 card=0x98021849 chip=0x98021002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    class      = display
    subclass   = VGA
none0@pci0:0:1:1:    class=0x040300 card=0x13141849 chip=0x13141002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    class      = multimedia
    subclass   = HDA
pcib1@pci0:0:4:0:    class=0x060400 card=0x12341022 chip=0x15121022 rev=0x00 hdr=0x01
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = PCI-PCI
atapci0@pci0:0:17:0:    class=0x01018f card=0x43901849 chip=0x43901002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'Integrated SATA II Controller (SB700)'
    class      = mass storage
    subclass   = ATA
ohci0@pci0:0:18:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci0@pci0:0:18:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
ohci1@pci0:0:19:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci1@pci0:0:19:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
none1@pci0:0:20:0:    class=0x0c0500 card=0x43851849 chip=0x43851002 rev=0x42 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'ATI SMBus (ATI RD600/RS600)'
    class      = serial bus
    subclass   = SMBus
atapci1@pci0:0:20:1:    class=0x01018a card=0x439c1849 chip=0x439c1002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'PATA 133 Controller (SB7xx)'
    class      = mass storage
    subclass   = ATA
none2@pci0:0:20:2:    class=0x040300 card=0x18921849 chip=0x43831002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'IXP SB600 High Definition Audio Controller'
    class      = multimedia
    subclass   = HDA
isab0@pci0:0:20:3:    class=0x060100 card=0x439d1849 chip=0x439d1002 rev=0x40 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 LPC host controller'
    class      = bridge
    subclass   = PCI-ISA
pcib2@pci0:0:20:4:    class=0x060401 card=0x00000000 chip=0x43841002 rev=0x40 hdr=0x01
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'IXP SB600 PCI to PCI Bridge'
    class      = bridge
    subclass   = PCI-PCI
ohci2@pci0:0:20:5:    class=0x0c0310 card=0x43991849 chip=0x43991002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB OHCI2 Controller'
    class      = serial bus
    subclass   = USB
pcib3@pci0:0:21:0:    class=0x060400 card=0x00001002 chip=0x43a01002 rev=0x00 hdr=0x01
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    class      = bridge
    subclass   = PCI-PCI
pcib4@pci0:0:21:1:    class=0x060400 card=0x00001002 chip=0x43a11002 rev=0x00 hdr=0x01
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    class      = bridge
    subclass   = PCI-PCI
ohci3@pci0:0:22:0:    class=0x0c0310 card=0x43971849 chip=0x43971002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB OHCI0 Controller'
    class      = serial bus
    subclass   = USB
ehci2@pci0:0:22:2:    class=0x0c0320 card=0x43961849 chip=0x43961002 rev=0x00 hdr=0x00
    vendor     = 'ATI Technologies Inc. / Advanced Micro Devices, Inc.'
    device     = 'SB700 USB EHCI Controller'
    class      = serial bus
    subclass   = USB
hostb1@pci0:0:24:0:    class=0x060000 card=0x00000000 chip=0x17001022 rev=0x43 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb2@pci0:0:24:1:    class=0x060000 card=0x00000000 chip=0x17011022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb3@pci0:0:24:2:    class=0x060000 card=0x00000000 chip=0x17021022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb4@pci0:0:24:3:    class=0x060000 card=0x00000000 chip=0x17031022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb5@pci0:0:24:4:    class=0x060000 card=0x00000000 chip=0x17041022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb6@pci0:0:24:5:    class=0x060000 card=0x00000000 chip=0x17181022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb7@pci0:0:24:6:    class=0x060000 card=0x00000000 chip=0x17161022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
hostb8@pci0:0:24:7:    class=0x060000 card=0x00000000 chip=0x17191022 rev=0x00 hdr=0x00
    vendor     = 'Advanced Micro Devices (AMD)'
    class      = bridge
    subclass   = HOST-PCI
re0@pci0:4:0:0:    class=0x020000 card=0x81681849 chip=0x816810ec rev=0x06 hdr=0x00
    vendor     = 'Realtek Semiconductor'
    device     = 'Gigabit Ethernet NIC(NDIS 6.0) (RTL8168/8111/8111c)'
    class      = network
    subclass   = ethernet